| /arch/riscv/kernel/ |
| A D | vector.c | 115 void *datap; in riscv_v_thread_zalloc() local 117 datap = kmem_cache_zalloc(cache, GFP_KERNEL); in riscv_v_thread_zalloc() 118 if (!datap) in riscv_v_thread_zalloc() 121 ctx->datap = datap; in riscv_v_thread_zalloc() 122 memset(ctx, 0, offsetof(struct __riscv_v_ext_state, datap)); in riscv_v_thread_zalloc() 135 if (tsk->thread.vstate.datap) in riscv_v_thread_free() 136 kmem_cache_free(riscv_v_user_cachep, tsk->thread.vstate.datap); in riscv_v_thread_free() 138 if (tsk->thread.kernel_vstate.datap) in riscv_v_thread_free() 139 kmem_cache_free(riscv_v_kernel_cachep, tsk->thread.kernel_vstate.datap); in riscv_v_thread_free() 208 WARN_ON(current->thread.vstate.datap); in riscv_v_first_use_handler()
|
| A D | signal.c | 77 void __user *datap; in save_v_state() local 84 datap = state + 1; in save_v_state() 87 WARN_ON(!IS_ALIGNED((unsigned long)datap, 16)); in save_v_state() 95 offsetof(struct __riscv_v_ext_state, datap)); in save_v_state() 97 err |= __put_user((__force void *)datap, &state->v_state.datap); in save_v_state() 99 err |= __copy_to_user(datap, current->thread.vstate.datap, riscv_v_vsize); in save_v_state() 120 void __user *datap; in __restore_v_state() local 131 offsetof(struct __riscv_v_ext_state, datap)); in __restore_v_state() 136 err = __get_user(datap, &state->v_state.datap); in __restore_v_state() 143 return copy_from_user(current->thread.vstate.datap, datap, riscv_v_vsize); in __restore_v_state()
|
| A D | kernel_mode_vector.c | 129 if (!kvstate->datap) in riscv_v_start_kernel_context() 137 __riscv_v_vstate_save(kvstate, kvstate->datap); in riscv_v_start_kernel_context() 148 __riscv_v_vstate_save(uvstate, uvstate->datap); in riscv_v_start_kernel_context() 183 __riscv_v_vstate_restore(vstate, vstate->datap); in riscv_v_context_nesting_end()
|
| A D | ptrace.c | 121 return membuf_write(&to, vstate->datap, riscv_v_vsize); in riscv_vr_get() 152 ret = user_regset_copyin(&pos, &count, &kbuf, &ubuf, vstate->datap, in riscv_vr_set()
|
| A D | process.c | 183 kfree(current->thread.vstate.datap); in flush_thread()
|
| /arch/riscv/kvm/ |
| A D | vcpu_vector.c | 30 WARN_ON(!cntx->vector.datap); in kvm_riscv_vcpu_vector_reset() 31 memset(cntx->vector.datap, 0, riscv_v_vsize); in kvm_riscv_vcpu_vector_reset() 78 vcpu->arch.guest_context.vector.datap = kzalloc(riscv_v_vsize, GFP_KERNEL); in kvm_riscv_vcpu_alloc_vector_context() 79 if (!vcpu->arch.guest_context.vector.datap) in kvm_riscv_vcpu_alloc_vector_context() 82 vcpu->arch.host_context.vector.datap = kzalloc(riscv_v_vsize, GFP_KERNEL); in kvm_riscv_vcpu_alloc_vector_context() 83 if (!vcpu->arch.host_context.vector.datap) in kvm_riscv_vcpu_alloc_vector_context() 91 kfree(vcpu->arch.guest_context.vector.datap); in kvm_riscv_vcpu_free_vector_context() 92 kfree(vcpu->arch.host_context.vector.datap); in kvm_riscv_vcpu_free_vector_context() 123 case KVM_REG_RISCV_VECTOR_CSR_REG(datap): in kvm_riscv_vcpu_vreg_addr() 130 *reg_addr = cntx->vector.datap + in kvm_riscv_vcpu_vreg_addr()
|
| A D | vcpu.c | 60 void *vector_datap = cntx->vector.datap; in kvm_riscv_vcpu_context_reset() 67 cntx->vector.datap = vector_datap; in kvm_riscv_vcpu_context_reset()
|
| /arch/m68k/kernel/ |
| A D | ptrace.c | 170 unsigned long __user *datap = (unsigned long __user *) data; in arch_ptrace() local 198 ret = put_user(tmp, datap); in arch_ptrace() 230 ret = put_user(tmp, datap); in arch_ptrace() 233 datap++; in arch_ptrace() 239 ret = get_user(tmp, datap); in arch_ptrace() 247 datap++; in arch_ptrace() 252 if (copy_to_user(datap, &child->thread.fp, in arch_ptrace() 258 if (copy_from_user(&child->thread.fp, datap, in arch_ptrace() 264 ret = put_user(task_thread_info(child)->tp_value, datap); in arch_ptrace()
|
| /arch/riscv/include/asm/ |
| A D | vector.h | 196 void *datap) in __riscv_v_vstate_save() argument 213 : : "r" (datap) : "memory", "t0", "t4"); in __riscv_v_vstate_save() 227 : "=&r" (vl) : "r" (datap) : "memory"); in __riscv_v_vstate_save() 233 void *datap) in __riscv_v_vstate_restore() argument 249 : : "r" (datap) : "memory", "t0", "t4"); in __riscv_v_vstate_restore() 263 : "=&r" (vl) : "r" (datap) : "memory"); in __riscv_v_vstate_restore() 309 __riscv_v_vstate_save(vstate, vstate->datap); in riscv_v_vstate_save() 318 __riscv_v_vstate_restore(vstate, vstate->datap); in riscv_v_vstate_restore() 381 prev->thread.kernel_vstate.datap); in __switch_to_vector()
|
| A D | kvm_vcpu_vector.h | 21 __riscv_v_vstate_save(&context->vector, context->vector.datap); in __kvm_riscv_vector_save() 26 __riscv_v_vstate_restore(&context->vector, context->vector.datap); in __kvm_riscv_vector_restore()
|
| A D | simd.h | 43 if (IS_ENABLED(CONFIG_RISCV_ISA_V_PREEMPTIVE) && current->thread.kernel_vstate.datap) { in may_use_simd()
|
| /arch/arm64/kvm/ |
| A D | mmio.c | 15 void *datap = NULL; in kvm_mmio_write_buf() local 26 datap = &tmp.byte; in kvm_mmio_write_buf() 30 datap = &tmp.hword; in kvm_mmio_write_buf() 34 datap = &tmp.word; in kvm_mmio_write_buf() 38 datap = &tmp.dword; in kvm_mmio_write_buf() 42 memcpy(buf, datap, len); in kvm_mmio_write_buf()
|
| /arch/x86/um/ |
| A D | ptrace_32.c | 176 void __user *datap = (void __user *) data; in subarch_ptrace() local 182 datap); in subarch_ptrace() 187 datap); in subarch_ptrace() 192 datap); in subarch_ptrace() 197 datap); in subarch_ptrace()
|
| A D | ptrace_64.c | 196 void __user *datap = (void __user *) data; in subarch_ptrace() local 203 datap); in subarch_ptrace() 208 datap); in subarch_ptrace()
|
| /arch/xtensa/kernel/ |
| A D | ptrace.c | 415 long __user *datap) in ptrace_gethbpregs() argument 442 if (copy_to_user(datap, user_data, sizeof(user_data))) in ptrace_gethbpregs() 449 long __user *datap) in ptrace_sethbpregs() argument 501 void __user *datap = (void __user *) data; in arch_ptrace() local 505 ret = ptrace_peekusr(child, addr, datap); in arch_ptrace() 513 ret = ptrace_getregs(child, datap); in arch_ptrace() 517 ret = ptrace_setregs(child, datap); in arch_ptrace() 521 ret = ptrace_getxregs(child, datap); in arch_ptrace() 525 ret = ptrace_setxregs(child, datap); in arch_ptrace() 529 ret = ptrace_gethbpregs(child, addr, datap); in arch_ptrace() [all …]
|
| /arch/x86/kernel/ |
| A D | ptrace.c | 785 datap); in arch_ptrace() 792 datap); in arch_ptrace() 799 datap); in arch_ptrace() 806 datap); in arch_ptrace() 1088 datap); in ia32_arch_ptrace() 1094 datap); in ia32_arch_ptrace() 1100 datap); in ia32_arch_ptrace() 1111 datap); in ia32_arch_ptrace() 1117 datap); in ia32_arch_ptrace() 1188 datap); in x32_arch_ptrace() [all …]
|
| /arch/sh/kernel/ |
| A D | ptrace_32.c | 341 unsigned long __user *datap = (unsigned long __user *)data; in arch_ptrace() local 384 ret = put_user(tmp, datap); in arch_ptrace() 417 datap); in arch_ptrace() 422 datap); in arch_ptrace() 428 datap); in arch_ptrace() 433 datap); in arch_ptrace() 440 datap); in arch_ptrace() 445 datap); in arch_ptrace()
|
| /arch/sh/lib/ |
| A D | io.c | 14 void __raw_readsl(const volatile void __iomem *addr, void *datap, int len) in __raw_readsl() argument 18 for (data = datap; (len != 0) && (((u32)data & 0x1f) != 0); len--) in __raw_readsl()
|
| /arch/arm/kernel/ |
| A D | ptrace.c | 729 unsigned long __user *datap = (unsigned long __user *) data; in arch_ptrace() local 733 ret = ptrace_read_user(child, addr, datap); in arch_ptrace() 744 datap); in arch_ptrace() 751 datap); in arch_ptrace() 758 datap); in arch_ptrace() 765 datap); in arch_ptrace() 770 ret = ptrace_getwmmxregs(child, datap); in arch_ptrace() 774 ret = ptrace_setwmmxregs(child, datap); in arch_ptrace() 780 datap); in arch_ptrace() 795 datap); in arch_ptrace() [all …]
|
| /arch/parisc/kernel/ |
| A D | ptrace.c | 125 unsigned long __user *datap = (unsigned long __user *)data; in arch_ptrace() local 144 ret = put_user(tmp, datap); in arch_ptrace() 191 datap); in arch_ptrace() 198 datap); in arch_ptrace() 205 datap); in arch_ptrace() 212 datap); in arch_ptrace()
|
| /arch/riscv/include/uapi/asm/ |
| A D | ptrace.h | 106 void *datap; member
|
| /arch/arm64/include/uapi/asm/ |
| A D | sigcontext.h | 138 __u64 datap; /* 16-byte aligned pointer to extra space cast to __u64 */ member
|
| /arch/arm64/kernel/ |
| A D | ptrace.c | 2213 void __user *datap = compat_ptr(data); in compat_arch_ptrace() local 2218 ret = compat_ptrace_read_user(child, addr, datap); in compat_arch_ptrace() 2230 datap); in compat_arch_ptrace() 2238 datap); in compat_arch_ptrace() 2243 (compat_ulong_t __user *)datap); in compat_arch_ptrace() 2256 datap); in compat_arch_ptrace() 2264 datap); in compat_arch_ptrace() 2269 ret = compat_ptrace_gethbpregs(child, addr, datap); in compat_arch_ptrace() 2273 ret = compat_ptrace_sethbpregs(child, addr, datap); in compat_arch_ptrace()
|
| A D | signal.c | 896 __get_user_error(extra_datap, &extra->datap, err); in parse_user_sigframe() 1337 __put_user_error(extra_datap, &extra->datap, err); in setup_sigframe()
|
| /arch/loongarch/kernel/ |
| A D | ptrace.c | 1005 unsigned long __user *datap = (void __user *) data; in arch_ptrace() local 1009 ret = read_user(child, addr, datap); in arch_ptrace()
|