Searched refs:datap (Results 1 - 25 of 74) sorted by last modified time

123

/linux-master/arch/riscv/kernel/
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 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 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...]
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);
/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/drivers/scsi/lpfc/
H A Dlpfc_sli.c22178 * @datap: Pointer to where data will be copied to.
22193 lpfc_read_object(struct lpfc_hba *phba, char *rdobject, uint32_t *datap, argument
22276 lpfc_sli_pcimem_bcopy(pcmd->virt, datap, byte_cnt);
H A Dlpfc_els.c8021 uint32_t *lp, *datap; local
8080 datap = lp;
8082 nportid = *datap++;
/linux-master/drivers/base/
H A Dplatform-msi.c148 struct platform_msi_priv_data *datap; local
173 datap = kzalloc(sizeof(*datap), GFP_KERNEL);
174 if (!datap)
177 datap->devid = ida_alloc_max(&platform_msi_devid_ida,
179 if (datap->devid < 0) {
180 err = datap->devid;
181 kfree(datap);
185 datap->write_msg = write_msi_msg;
186 datap
[all...]
/linux-master/arch/riscv/include/asm/
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
H A Dsimd.h43 if (IS_ENABLED(CONFIG_RISCV_ISA_V_PREEMPTIVE) && current->thread.kernel_vstate.datap) {
/linux-master/drivers/s390/block/
H A Ddasd_eckd.c5519 char *datap; local
5528 datap = (char *)*((addr_t *)dma32_to_virt(from->cda));
5530 datap = dma32_to_virt(from->cda);
5540 len += sprintf(page + len, "%02x", datap[count]);
/linux-master/tools/testing/selftests/arm64/signal/testcases/
H A Dtestcases.c46 if (extra->datap & 0x0fUL)
50 else if (extra->datap != (uint64_t)term + 0x10UL)
55 *extra_data = (void *)extra->datap;
/linux-master/tools/perf/util/
H A Dexpr.c244 struct expr_id_data **datap)
248 if (expr__get_id(ctx, id, datap) || !*datap) {
253 data = *datap;
243 expr__resolve_id(struct expr_parse_ctx *ctx, const char *id, struct expr_id_data **datap) argument
/linux-master/kernel/
H A Dptrace.c1322 compat_ulong_t __user *datap = compat_ptr(data); local
1335 ret = put_user(word, datap);
1346 ret = put_user((compat_ulong_t) child->ptrace_message, datap);
1353 (struct compat_siginfo __user *) datap,
1359 &siginfo, (struct compat_siginfo __user *) datap);
1369 (struct compat_iovec __user *) datap;
/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/security/selinux/ss/
H A Dpolicydb.c315 static int (*const destroy_f[SYM_NUM])(void *key, void *datum, void *datap) = {
543 static int common_index(void *key, void *datum, void *datap) argument
549 p = datap;
558 static int class_index(void *key, void *datum, void *datap) argument
564 p = datap;
573 static int role_index(void *key, void *datum, void *datap) argument
579 p = datap;
589 static int type_index(void *key, void *datum, void *datap) argument
595 p = datap;
608 static int user_index(void *key, void *datum, void *datap) argument
624 sens_index(void *key, void *datum, void *datap) argument
643 cat_index(void *key, void *datum, void *datap) argument
1674 user_bounds_sanity_check(void *key, void *datum, void *datap) argument
1711 role_bounds_sanity_check(void *key, void *datum, void *datap) argument
1748 type_bounds_sanity_check(void *key, void *datum, void *datap) argument
[all...]
H A Dconditional.c182 int cond_index_bool(void *key, void *datum, void *datap) argument
188 p = datap;
H A Dconditional.h69 int cond_index_bool(void *key, void *datum, void *datap);
/linux-master/fs/lockd/
H A Dsvcsubs.c461 nlmsvc_match_sb(void *datap, struct nlm_file *file) argument
463 struct super_block *sb = datap;
485 nlmsvc_match_ip(void *datap, struct nlm_host *host) argument
487 return rpc_cmp_addr(nlm_srcaddr(host), datap);
/linux-master/tools/testing/selftests/riscv/vector/
H A Dv_initval_nolibc.c26 char *datap, *tmp; local
28 datap = malloc(MAX_VSIZE);
29 if (!datap) {
34 tmp = datap;
47 : "=&r" (vl), "=r" (tmp) : "r" (datap) : "memory");
51 if (datap[0] != 0x00 && datap[0] != 0xff) {
53 dump(datap, vl * 4);
58 if (datap[i] != datap[
[all...]
/linux-master/arch/x86/um/
H A Dptrace_32.c236 void __user *datap = (void __user *) data; local
239 ret = get_fpregs(datap, child);
242 ret = set_fpregs(datap, child);
245 ret = get_fpxregs(datap, child);
248 ret = set_fpxregs(datap, child);
H A Dptrace_64.c225 void __user *datap = (void __user *) data; local
229 ret = get_fpregs(datap, child);
232 ret = set_fpregs(datap, child);
/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 397 milliseconds

123