/linux-master/arch/sh/lib/ |
H A D | io.c | 14 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 D | recov_avx512.c | 371 .datap = raid6_datap_recov_avx512,
|
H A D | recov_s390xc.c | 113 .datap = raid6_datap_recov_s390xc,
|
/linux-master/tools/virtio/ringtest/ |
H A D | noring.c | 12 int add_inbuf(unsigned len, void *buf, void *datap) argument
|
H A D | ptr_ring.c | 128 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 D | ring.c | 112 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 D | virtio_ring_0_9.c | 99 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 D | ptrace.c | 729 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 D | sigcontext.h | 118 * 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 D | ptrace.c | 2080 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 D | signal.c | 741 __get_user_error(extra_datap, &extra->datap, err); 1085 __put_user_error(extra_datap, &extra->datap, err);
|
/linux-master/arch/arm64/kvm/ |
H A D | mmio.c | 15 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 D | ptrace.c | 995 unsigned long __user *datap = (void __user *) data; local 999 ret = read_user(child, addr, datap);
|
/linux-master/arch/m68k/kernel/ |
H A D | ptrace.c | 170 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 D | ptrace.c | 125 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 D | kvm_vcpu_vector.h | 21 __riscv_v_vstate_save(&context->vector, context->vector.datap); 26 __riscv_v_vstate_restore(&context->vector, context->vector.datap);
|
H A D | simd.h | 43 if (IS_ENABLED(CONFIG_RISCV_ISA_V_PREEMPTIVE) && current->thread.kernel_vstate.datap) {
|
H A D | vector.h | 104 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 D | ptrace.h | 106 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 D | kernel_mode_vector.c | 129 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 D | process.c | 170 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 D | ptrace.c | 118 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 D | signal.c | 77 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 D | vector.c | 105 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 D | vcpu_vector.c | 27 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...] |