/linux-master/arch/riscv/kernel/ |
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 | 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 | 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...] |
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);
|
/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/drivers/scsi/lpfc/ |
H A D | lpfc_sli.c | 22178 * @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 D | lpfc_els.c | 8021 uint32_t *lp, *datap; local 8080 datap = lp; 8082 nportid = *datap++;
|
/linux-master/drivers/base/ |
H A D | platform-msi.c | 148 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 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
|
H A D | simd.h | 43 if (IS_ENABLED(CONFIG_RISCV_ISA_V_PREEMPTIVE) && current->thread.kernel_vstate.datap) {
|
/linux-master/drivers/s390/block/ |
H A D | dasd_eckd.c | 5519 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 D | testcases.c | 46 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 D | expr.c | 244 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 D | ptrace.c | 1322 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 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/security/selinux/ss/ |
H A D | policydb.c | 315 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 D | conditional.c | 182 int cond_index_bool(void *key, void *datum, void *datap) argument 188 p = datap;
|
H A D | conditional.h | 69 int cond_index_bool(void *key, void *datum, void *datap);
|
/linux-master/fs/lockd/ |
H A D | svcsubs.c | 461 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 D | v_initval_nolibc.c | 26 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 D | ptrace_32.c | 236 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 D | ptrace_64.c | 225 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 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...] |