Home
last modified time | relevance | path

Searched refs:xbuf (Results 1 - 24 of 24) sorted by relevance

/kernel/linux/linux-6.6/tools/testing/selftests/x86/
H A Damx.c52 static inline void xsave(struct xsave_buffer *xbuf, uint64_t rfbm) in xsave() argument
58 : : "D" (xbuf), "a" (rfbm_lo), "d" (rfbm_hi) in xsave()
62 static inline void xrstor(struct xsave_buffer *xbuf, uint64_t rfbm) in xrstor() argument
68 : : "D" (xbuf), "a" (rfbm_lo), "d" (rfbm_hi)); in xrstor()
168 struct xsave_buffer *xbuf; in alloc_xbuf() local
171 xbuf = aligned_alloc(64, xbuf_size); in alloc_xbuf()
172 if (!xbuf) in alloc_xbuf()
174 return xbuf; in alloc_xbuf()
194 static void set_rand_tiledata(struct xsave_buffer *xbuf) in set_rand_tiledata() argument
196 int *ptr = (int *)&xbuf in set_rand_tiledata()
260 void *xbuf = ctx->uc_mcontext.fpregs; handle_noperm() local
309 xrstor_safe(struct xsave_buffer *xbuf, uint64_t mask) xrstor_safe() argument
334 load_rand_tiledata(struct xsave_buffer *xbuf) load_rand_tiledata() argument
620 validate_tiledata_regs_same(struct xsave_buffer *xbuf) validate_tiledata_regs_same() argument
628 validate_tiledata_regs_changed(struct xsave_buffer *xbuf) validate_tiledata_regs_changed() argument
701 struct xsave_buffer *xbuf; check_tiledata() local
857 struct xsave_buffer *xbuf; ptracer_inject_tiledata() local
[all...]
/kernel/linux/linux-5.10/drivers/gpu/drm/nouveau/nvkm/subdev/i2c/
H A Dauxgm200.c83 u32 xbuf[4] = {}; in gm200_i2c_aux_xfer() local
100 memcpy(xbuf, data, *size); in gm200_i2c_aux_xfer()
102 AUX_TRACE(&aux->base, "wr %08x", xbuf[i / 4]); in gm200_i2c_aux_xfer()
103 nvkm_wr32(device, 0x00d930 + base + i, xbuf[i / 4]); in gm200_i2c_aux_xfer()
151 xbuf[i / 4] = nvkm_rd32(device, 0x00d940 + base + i); in gm200_i2c_aux_xfer()
152 AUX_TRACE(&aux->base, "rd %08x", xbuf[i / 4]); in gm200_i2c_aux_xfer()
154 memcpy(data, xbuf, *size); in gm200_i2c_aux_xfer()
H A Dauxg94.c83 u32 xbuf[4] = {}; in g94_i2c_aux_xfer() local
100 memcpy(xbuf, data, *size); in g94_i2c_aux_xfer()
102 AUX_TRACE(&aux->base, "wr %08x", xbuf[i / 4]); in g94_i2c_aux_xfer()
103 nvkm_wr32(device, 0x00e4c0 + base + i, xbuf[i / 4]); in g94_i2c_aux_xfer()
151 xbuf[i / 4] = nvkm_rd32(device, 0x00e4d0 + base + i); in g94_i2c_aux_xfer()
152 AUX_TRACE(&aux->base, "rd %08x", xbuf[i / 4]); in g94_i2c_aux_xfer()
154 memcpy(data, xbuf, *size); in g94_i2c_aux_xfer()
/kernel/linux/linux-5.10/security/keys/
H 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()
/kernel/linux/linux-6.6/security/keys/
H 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()
/kernel/linux/linux-6.6/drivers/gpu/drm/nouveau/nvkm/subdev/i2c/
H 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()
H 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()
/kernel/linux/linux-6.6/fs/xfs/scrub/
H A Dxfile.h74 struct xfile_page *xbuf);
75 int xfile_put_page(struct xfile *xf, struct xfile_page *xbuf);
/kernel/linux/linux-5.10/crypto/
H A Dtcrypt.c113 static void sg_init_aead(struct scatterlist *sg, char *xbuf[XBUFSIZE], in sg_init_aead() argument
134 sg_set_buf(&sg[k + 1], xbuf[k], PAGE_SIZE); in sg_init_aead()
137 sg_set_buf(&sg[k + 1], xbuf[k], rem); in sg_init_aead()
152 char *xbuf[XBUFSIZE]; member
295 if (testmgr_alloc_buf(data[i].xbuf)) { in test_mb_aead_speed()
297 testmgr_free_buf(data[i].xbuf); in test_mb_aead_speed()
382 sg_init_aead(cur->sg, cur->xbuf, in test_mb_aead_speed()
445 testmgr_free_buf(data[i].xbuf); in test_mb_aead_speed()
534 char *xbuf[XBUFSIZE]; in test_aead_speed() local
555 if (testmgr_alloc_buf(xbuf)) in test_aead_speed()
719 char *xbuf[XBUFSIZE]; global() member
1152 char *xbuf[XBUFSIZE]; global() member
[all...]
H A Dtestmgr.c2621 char *xbuf[XBUFSIZE]; in test_cipher() local
2624 if (testmgr_alloc_buf(xbuf)) in test_cipher()
2646 data = xbuf[0]; in test_cipher()
2693 testmgr_free_buf(xbuf); in test_cipher()
3933 char *xbuf[XBUFSIZE]; in test_akcipher_one() local
3946 if (testmgr_alloc_buf(xbuf)) in test_akcipher_one()
4002 memcpy(xbuf[0], m, m_size); in test_akcipher_one()
4005 sg_set_buf(&src_tab[0], xbuf[0], 8); in test_akcipher_one()
4006 sg_set_buf(&src_tab[1], xbuf[0] + 8, m_size - 8); in test_akcipher_one()
4010 memcpy(xbuf[ in test_akcipher_one()
[all...]
/kernel/linux/linux-5.10/sound/core/seq/
H 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()
/kernel/linux/linux-6.6/sound/core/seq/
H 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()
H A Dseq_ump_convert.c1151 u8 buf[6], *xbuf; in cvt_sysex_to_ump() local
1166 xbuf = buf; in cvt_sysex_to_ump()
1167 if (*xbuf == UMP_MIDI1_MSG_SYSEX_START) { in cvt_sysex_to_ump()
1169 xbuf++; in cvt_sysex_to_ump()
1171 if (len > 0 && xbuf[len - 1] == UMP_MIDI1_MSG_SYSEX_END) { in cvt_sysex_to_ump()
1176 if (xbuf[len - 1] == UMP_MIDI1_MSG_SYSEX_END) { in cvt_sysex_to_ump()
1183 fill_sysex7_ump(dest_port, ev_cvt.ump, status, xbuf, len); in cvt_sysex_to_ump()
/kernel/linux/linux-5.10/drivers/misc/genwqe/
H 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, tocop in do_flash_read()
[all...]
/kernel/linux/linux-6.6/drivers/misc/genwqe/
H 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, tocop in do_flash_read()
[all...]
/kernel/linux/linux-6.6/crypto/
H A Dtcrypt.c105 static void sg_init_aead(struct scatterlist *sg, char *xbuf[XBUFSIZE], in sg_init_aead() argument
126 sg_set_buf(&sg[k + 1], xbuf[k], PAGE_SIZE); in sg_init_aead()
129 sg_set_buf(&sg[k + 1], xbuf[k], rem); in sg_init_aead()
144 char *xbuf[XBUFSIZE]; member
292 if (testmgr_alloc_buf(data[i].xbuf)) { in test_mb_aead_speed()
294 testmgr_free_buf(data[i].xbuf); in test_mb_aead_speed()
381 sg_init_aead(cur->sg, cur->xbuf, in test_mb_aead_speed()
444 testmgr_free_buf(data[i].xbuf); in test_mb_aead_speed()
533 char *xbuf[XBUFSIZE]; in test_aead_speed() local
554 if (testmgr_alloc_buf(xbuf)) in test_aead_speed()
963 char *xbuf[XBUFSIZE]; global() member
[all...]
H A Dtestmgr.c2731 char *xbuf[XBUFSIZE]; in test_cipher() local
2734 if (testmgr_alloc_buf(xbuf)) in test_cipher()
2756 data = xbuf[0]; in test_cipher()
2803 testmgr_free_buf(xbuf); in test_cipher()
4078 char *xbuf[XBUFSIZE]; in test_akcipher_one() local
4091 if (testmgr_alloc_buf(xbuf)) in test_akcipher_one()
4147 memcpy(xbuf[0], m, m_size); in test_akcipher_one()
4150 sg_set_buf(&src_tab[0], xbuf[0], 8); in test_akcipher_one()
4151 sg_set_buf(&src_tab[1], xbuf[0] + 8, m_size - 8); in test_akcipher_one()
4155 memcpy(xbuf[ in test_akcipher_one()
[all...]
/kernel/linux/linux-6.6/arch/x86/kernel/fpu/
H 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()
/kernel/linux/linux-5.10/arch/x86/kernel/fpu/
H A Dxstate.c1337 u8 *xbuf = (u8 *)xstate; in copy_supervisor_to_kernel() local
1343 memmove(xbuf + xstate_comp_offsets[i], in copy_supervisor_to_kernel()
1344 xbuf + xstate_supervisor_only_offsets[i], in copy_supervisor_to_kernel()
/kernel/linux/linux-5.10/drivers/usb/gadget/function/
H A Drndis.c711 u8 *xbuf; in rndis_reset_response() local
715 while ((xbuf = rndis_get_next_response(params, &length))) in rndis_reset_response()
716 rndis_free_response(params, xbuf); in rndis_reset_response()
/kernel/linux/linux-6.6/drivers/usb/gadget/function/
H 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()
/kernel/linux/linux-6.6/drivers/crypto/aspeed/
H A Daspeed-acry.c248 const void *xbuf, size_t nbytes, in aspeed_acry_rsa_ctx_copy()
251 const u8 *src = xbuf; in aspeed_acry_rsa_ctx_copy()
247 aspeed_acry_rsa_ctx_copy(struct aspeed_acry_dev *acry_dev, void *buf, const void *xbuf, size_t nbytes, enum aspeed_rsa_key_mode mode) aspeed_acry_rsa_ctx_copy() argument
/kernel/linux/linux-5.10/drivers/net/hyperv/
H A Dnetvsc_drv.c823 void *xbuf = xdp->data_hard_start; in netvsc_alloc_recv_skb() local
826 if (xbuf) { in netvsc_alloc_recv_skb()
831 skb = build_skb(xbuf, frag_size); in netvsc_alloc_recv_skb()
834 __free_page(virt_to_page(xbuf)); in netvsc_alloc_recv_skb()
/kernel/linux/linux-6.6/drivers/net/hyperv/
H A Dnetvsc_drv.c796 void *xbuf = xdp->data_hard_start; in netvsc_alloc_recv_skb() local
799 if (xbuf) { in netvsc_alloc_recv_skb()
804 skb = build_skb(xbuf, frag_size); in netvsc_alloc_recv_skb()
807 __free_page(virt_to_page(xbuf)); in netvsc_alloc_recv_skb()

Completed in 35 milliseconds