Searched refs:datap (Results 1 - 25 of 74) sorted by path

123

/linux-master/arch/sh/lib/
H A Dio.c14 void __raw_readsl(const void __iomem *addr, void *datap, int len) argument
18 for (data = datap; (len != 0) && (((u32)data & 0x1f) != 0); len--)
/linux-master/lib/raid6/
H A Drecov_avx512.c371 .datap = raid6_datap_recov_avx512,
H A Drecov_s390xc.c113 .datap = raid6_datap_recov_s390xc,
/linux-master/tools/virtio/ringtest/
H A Dnoring.c12 int add_inbuf(unsigned len, void *buf, void *datap) argument
H A Dptr_ring.c128 int add_inbuf(unsigned len, void *buf, void *datap) argument
149 void *datap; local
152 datap = NULL;
154 datap = "Buffer\n";
158 return datap;
H A Dring.c112 int add_inbuf(unsigned len, void *buf, void *datap) argument
135 data[index].data = datap;
147 void *datap; local
155 datap = data[index].data;
161 return datap;
H A Dvirtio_ring_0_9.c99 int add_inbuf(unsigned len, void *buf, void *datap) argument
130 data[head].data = datap;
156 void *datap; local
185 datap = data[index].data;
194 return datap;
/linux-master/arch/arm/kernel/
H A Dptrace.c729 unsigned long __user *datap = (unsigned long __user *) data; local
733 ret = ptrace_read_user(child, addr, datap);
744 datap);
751 datap);
758 datap);
765 datap);
770 ret = ptrace_getwmmxregs(child, datap);
774 ret = ptrace_setwmmxregs(child, datap);
780 datap);
795 datap);
[all...]
/linux-master/arch/arm64/include/uapi/asm/
H A Dsigcontext.h118 * 4) The extra space to which datap points must start at the first
131 __u64 datap; /* 16-byte aligned pointer to extra space cast to __u64 */ member in struct:extra_context
/linux-master/arch/arm64/kernel/
H A Dptrace.c2080 void __user *datap = compat_ptr(data); local
2085 ret = compat_ptrace_read_user(child, addr, datap);
2097 datap);
2105 datap);
2110 (compat_ulong_t __user *)datap);
2123 datap);
2131 datap);
2136 ret = compat_ptrace_gethbpregs(child, addr, datap);
2140 ret = compat_ptrace_sethbpregs(child, addr, datap);
H A Dsignal.c741 __get_user_error(extra_datap, &extra->datap, err);
1085 __put_user_error(extra_datap, &extra->datap, err);
/linux-master/arch/arm64/kvm/
H A Dmmio.c15 void *datap = NULL; local
26 datap = &tmp.byte;
30 datap = &tmp.hword;
34 datap = &tmp.word;
38 datap = &tmp.dword;
42 memcpy(buf, datap, len);
/linux-master/arch/loongarch/kernel/
H A Dptrace.c995 unsigned long __user *datap = (void __user *) data; local
999 ret = read_user(child, addr, datap);
/linux-master/arch/m68k/kernel/
H A Dptrace.c170 unsigned long __user *datap = (unsigned long __user *) data; local
198 ret = put_user(tmp, datap);
230 ret = put_user(tmp, datap);
233 datap++;
239 ret = get_user(tmp, datap);
247 datap++;
252 if (copy_to_user(datap, &child->thread.fp,
258 if (copy_from_user(&child->thread.fp, datap,
264 ret = put_user(task_thread_info(child)->tp_value, datap);
/linux-master/arch/parisc/kernel/
H A Dptrace.c125 unsigned long __user *datap = (unsigned long __user *)data; local
144 ret = put_user(tmp, datap);
191 datap);
198 datap);
205 datap);
212 datap);
/linux-master/arch/riscv/include/asm/
H A Dkvm_vcpu_vector.h21 __riscv_v_vstate_save(&context->vector, context->vector.datap);
26 __riscv_v_vstate_restore(&context->vector, context->vector.datap);
H A Dsimd.h43 if (IS_ENABLED(CONFIG_RISCV_ISA_V_PREEMPTIVE) && current->thread.kernel_vstate.datap) {
H A Dvector.h104 void *datap)
122 : "=&r" (vl) : "r" (datap) : "memory");
127 void *datap)
144 : "=&r" (vl) : "r" (datap) : "memory");
181 __riscv_v_vstate_save(vstate, vstate->datap);
190 __riscv_v_vstate_restore(vstate, vstate->datap);
248 prev->thread.kernel_vstate.datap);
103 __riscv_v_vstate_save(struct __riscv_v_ext_state *save_to, void *datap) argument
126 __riscv_v_vstate_restore(struct __riscv_v_ext_state *restore_from, void *datap) argument
/linux-master/arch/riscv/include/uapi/asm/
H A Dptrace.h106 void *datap; member in struct:__riscv_v_ext_state
108 * In signal handler, datap will be set a correct user stack offset
109 * and vector registers will be copied to the address of datap
/linux-master/arch/riscv/kernel/
H A Dkernel_mode_vector.c129 if (!kvstate->datap)
137 __riscv_v_vstate_save(kvstate, kvstate->datap);
148 __riscv_v_vstate_save(uvstate, uvstate->datap);
183 __riscv_v_vstate_restore(vstate, vstate->datap);
H A Dprocess.c170 kfree(current->thread.vstate.datap);
178 /* Free the vector context of datap. */
187 /* clear entire V context, including datap for a new task */
H A Dptrace.c118 return membuf_write(&to, vstate->datap, riscv_v_vsize);
133 /* Copy rest of the vstate except datap */
149 ret = user_regset_copyin(&pos, &count, &kbuf, &ubuf, vstate->datap,
H A Dsignal.c77 void __user *datap; local
83 /* Point datap right after the end of __sc_riscv_v_state */
84 datap = state + 1;
86 /* datap is designed to be 16 byte aligned for better performance */
87 WARN_ON(unlikely(!IS_ALIGNED((unsigned long)datap, 16)));
93 /* Copy everything of vstate but datap. */
95 offsetof(struct __riscv_v_ext_state, datap));
96 /* Copy the pointer datap itself. */
97 err |= __put_user((__force void *)datap, &state->v_state.datap);
120 void __user *datap; local
[all...]
H A Dvector.c105 void *datap; local
107 datap = kmem_cache_zalloc(cache, GFP_KERNEL);
108 if (!datap)
111 ctx->datap = datap;
112 memset(ctx, 0, offsetof(struct __riscv_v_ext_state, datap));
125 if (tsk->thread.vstate.datap)
126 kmem_cache_free(riscv_v_user_cachep, tsk->thread.vstate.datap);
128 if (tsk->thread.kernel_vstate.datap)
129 kmem_cache_free(riscv_v_kernel_cachep, tsk->thread.kernel_vstate.datap);
[all...]
/linux-master/arch/riscv/kvm/
H A Dvcpu_vector.c27 WARN_ON(!cntx->vector.datap);
28 memset(cntx->vector.datap, 0, riscv_v_vsize);
76 cntx->vector.datap = kmalloc(riscv_v_vsize, GFP_KERNEL);
77 if (!cntx->vector.datap)
81 vcpu->arch.host_context.vector.datap = kzalloc(riscv_v_vsize, GFP_KERNEL);
82 if (!vcpu->arch.host_context.vector.datap)
90 kfree(vcpu->arch.guest_reset_context.vector.datap);
91 kfree(vcpu->arch.host_context.vector.datap);
122 case KVM_REG_RISCV_VECTOR_CSR_REG(datap):
129 *reg_addr = cntx->vector.datap
[all...]

Completed in 502 milliseconds

123