Home
last modified time | relevance | path

Searched refs:xbuf (Results 1 – 12 of 12) sorted by relevance

/linux-6.3-rc2/tools/testing/selftests/x86/
A Damx.c166 struct xsave_buffer *xbuf; in alloc_xbuf() local
170 if (!xbuf) in alloc_xbuf()
172 return xbuf; in alloc_xbuf()
310 xrstor(xbuf, mask); in xrstor_safe()
334 clear_xstate_header(xbuf); in load_rand_tiledata()
336 set_rand_tiledata(xbuf); in load_rand_tiledata()
694 struct xsave_buffer *xbuf; in check_tiledata() local
697 xbuf = alloc_xbuf(); in check_tiledata()
698 if (!xbuf) in check_tiledata()
705 load_rand_tiledata(xbuf); in check_tiledata()
[all …]
/linux-6.3-rc2/drivers/gpu/drm/nouveau/nvkm/subdev/i2c/
A Dauxgm200.c84 u32 xbuf[4] = {}; in gm200_i2c_aux_xfer() local
103 memcpy(xbuf, data, *size); in gm200_i2c_aux_xfer()
105 AUX_TRACE(&aux->base, "wr %08x", xbuf[i / 4]); in gm200_i2c_aux_xfer()
106 nvkm_wr32(device, 0x00d930 + base + i, xbuf[i / 4]); in gm200_i2c_aux_xfer()
154 xbuf[i / 4] = nvkm_rd32(device, 0x00d940 + base + i); in gm200_i2c_aux_xfer()
155 AUX_TRACE(&aux->base, "rd %08x", xbuf[i / 4]); in gm200_i2c_aux_xfer()
157 memcpy(data, xbuf, *size); in gm200_i2c_aux_xfer()
A Dauxg94.c84 u32 xbuf[4] = {}; in g94_i2c_aux_xfer() local
103 memcpy(xbuf, data, *size); in g94_i2c_aux_xfer()
105 AUX_TRACE(&aux->base, "wr %08x", xbuf[i / 4]); in g94_i2c_aux_xfer()
106 nvkm_wr32(device, 0x00e4c0 + base + i, xbuf[i / 4]); in g94_i2c_aux_xfer()
154 xbuf[i / 4] = nvkm_rd32(device, 0x00e4d0 + base + i); in g94_i2c_aux_xfer()
155 AUX_TRACE(&aux->base, "rd %08x", xbuf[i / 4]); in g94_i2c_aux_xfer()
157 memcpy(data, xbuf, *size); in g94_i2c_aux_xfer()
/linux-6.3-rc2/security/keys/
A Dproc.c160 char xbuf[16]; in proc_keys_show() local
202 memcpy(xbuf, "perm", 5); in proc_keys_show()
204 memcpy(xbuf, "expd", 5); in proc_keys_show()
209 sprintf(xbuf, "%llus", timo); in proc_keys_show()
211 sprintf(xbuf, "%llum", div_u64(timo, 60)); in proc_keys_show()
213 sprintf(xbuf, "%lluh", div_u64(timo, 60 * 60)); in proc_keys_show()
215 sprintf(xbuf, "%llud", div_u64(timo, 60 * 60 * 24)); in proc_keys_show()
217 sprintf(xbuf, "%lluw", div_u64(timo, 60 * 60 * 24 * 7)); in proc_keys_show()
236 xbuf, in proc_keys_show()
/linux-6.3-rc2/drivers/misc/genwqe/
A Dcard_dev.c511 u8 *xbuf; in do_flash_update() local
540 xbuf = __genwqe_alloc_consistent(cd, FLASH_BLOCK, &dma_addr); in do_flash_update()
541 if (xbuf == NULL) in do_flash_update()
554 rc = copy_from_user(xbuf, buf, tocopy); in do_flash_update()
559 crc = genwqe_crc32(xbuf, tocopy, 0xffffffff); in do_flash_update()
635 __genwqe_free_consistent(cd, FLASH_BLOCK, xbuf, dma_addr); in do_flash_update()
647 u8 *xbuf; in do_flash_read() local
676 xbuf = __genwqe_alloc_consistent(cd, FLASH_BLOCK, &dma_addr); in do_flash_read()
677 if (xbuf == NULL) in do_flash_read()
739 rc = copy_to_user(buf, xbuf, tocopy); in do_flash_read()
[all …]
/linux-6.3-rc2/sound/core/seq/
A Dseq_midi_event.c321 unsigned char xbuf[4]; in snd_midi_event_decode() local
328 xbuf[0] = cmd; in snd_midi_event_decode()
330 status_event[type].decode(ev, xbuf + 1); in snd_midi_event_decode()
335 status_event[type].decode(ev, xbuf + 0); in snd_midi_event_decode()
340 memcpy(buf, xbuf, qlen); in snd_midi_event_decode()
/linux-6.3-rc2/crypto/
A Dtcrypt.c141 char *xbuf[XBUFSIZE]; member
291 testmgr_free_buf(data[i].xbuf); in test_mb_aead_speed()
378 sg_init_aead(cur->sg, cur->xbuf, in test_mb_aead_speed()
441 testmgr_free_buf(data[i].xbuf); in test_mb_aead_speed()
530 char *xbuf[XBUFSIZE]; in test_aead_speed() local
551 if (testmgr_alloc_buf(xbuf)) in test_aead_speed()
693 testmgr_free_buf(xbuf); in test_aead_speed()
960 char *xbuf[XBUFSIZE]; member
1089 testmgr_free_buf(data[i].xbuf); in test_mb_skcipher_speed()
1172 memset(cur->xbuf[p], 0xff, k); in test_mb_skcipher_speed()
[all …]
A Dtestmgr.c2668 char *xbuf[XBUFSIZE]; in test_cipher() local
2671 if (testmgr_alloc_buf(xbuf)) in test_cipher()
2693 data = xbuf[0]; in test_cipher()
2740 testmgr_free_buf(xbuf); in test_cipher()
4006 char *xbuf[XBUFSIZE]; in test_akcipher_one() local
4019 if (testmgr_alloc_buf(xbuf)) in test_akcipher_one()
4075 memcpy(xbuf[0], m, m_size); in test_akcipher_one()
4083 memcpy(xbuf[1], c, c_size); in test_akcipher_one()
4143 memcpy(xbuf[0], c, c_size); in test_akcipher_one()
4145 sg_init_one(&src, xbuf[0], c_size); in test_akcipher_one()
[all …]
/linux-6.3-rc2/arch/x86/kernel/fpu/
A Dsignal.c210 struct xregs_state __user *xbuf = buf_fx; in copy_fpstate_to_sigframe() local
216 if (__clear_user(&xbuf->header, sizeof(xbuf->header))) in copy_fpstate_to_sigframe()
/linux-6.3-rc2/drivers/usb/gadget/function/
A Drndis.c682 u8 *xbuf; in rndis_reset_response() local
686 while ((xbuf = rndis_get_next_response(params, &length))) in rndis_reset_response()
687 rndis_free_response(params, xbuf); in rndis_reset_response()
/linux-6.3-rc2/drivers/crypto/aspeed/
A Daspeed-acry.c251 const void *xbuf, size_t nbytes, in aspeed_acry_rsa_ctx_copy() argument
254 const u8 *src = xbuf; in aspeed_acry_rsa_ctx_copy()
/linux-6.3-rc2/drivers/net/hyperv/
A Dnetvsc_drv.c792 void *xbuf = xdp->data_hard_start; in netvsc_alloc_recv_skb() local
795 if (xbuf) { in netvsc_alloc_recv_skb()
800 skb = build_skb(xbuf, frag_size); in netvsc_alloc_recv_skb()
803 __free_page(virt_to_page(xbuf)); in netvsc_alloc_recv_skb()

Completed in 31 milliseconds