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

123

/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/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/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/arch/riscv/include/asm/
H A Dsimd.h43 if (IS_ENABLED(CONFIG_RISCV_ISA_V_PREEMPTIVE) && current->thread.kernel_vstate.datap) {
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 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/kernel/
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 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 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/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...]
/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/drivers/net/wireless/ath/ath6kl/
H A Dwmi.c166 u8 *datap; local
188 datap = skb->data;
192 memcpy(datap, eth_hdr, sizeof(*eth_hdr));
194 llc_hdr = (struct ath6kl_llc_snap_hdr *)(datap + sizeof(*eth_hdr));
310 u8 *datap; local
315 datap = skb->data;
316 data_hdr = (struct wmi_data_hdr *) datap;
327 llc_hdr = (struct ath6kl_llc_snap_hdr *)(datap +
394 u8 *datap; local
400 datap
458 u8 *datap; local
478 ath6kl_wmi_tx_complete_event_rx(u8 *datap, int len) argument
503 ath6kl_wmi_remain_on_chnl_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) argument
535 ath6kl_wmi_cancel_remain_on_chnl_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) argument
573 ath6kl_wmi_tx_status_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) argument
599 ath6kl_wmi_rx_probe_req_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) argument
627 ath6kl_wmi_p2p_capabilities_event_rx(u8 *datap, int len) argument
642 ath6kl_wmi_rx_action_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) argument
666 ath6kl_wmi_p2p_info_event_rx(u8 *datap, int len) argument
741 ath6kl_wmi_ready_event_rx(struct wmi *wmi, u8 *datap, int len) argument
854 ath6kl_wmi_connect_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) argument
985 ath6kl_wmi_regdomain_event(struct wmi *wmi, u8 *datap, int len) argument
1020 ath6kl_wmi_disconnect_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) argument
1045 ath6kl_wmi_peer_node_event_rx(struct wmi *wmi, u8 *datap, int len) argument
1064 ath6kl_wmi_tkip_micerr_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) argument
1086 ath6kl_wmi_bssinfo_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) argument
1170 ath6kl_wmi_pstream_timeout_event_rx(struct wmi *wmi, u8 *datap, int len) argument
1201 ath6kl_wmi_bitrate_reply_rx(struct wmi *wmi, u8 *datap, int len) argument
1224 ath6kl_wmi_test_rx(struct wmi *wmi, u8 *datap, int len) argument
1231 ath6kl_wmi_ratemask_reply_rx(struct wmi *wmi, u8 *datap, int len) argument
1241 ath6kl_wmi_ch_list_reply_rx(struct wmi *wmi, u8 *datap, int len) argument
1251 ath6kl_wmi_tx_pwr_reply_rx(struct wmi *wmi, u8 *datap, int len) argument
1264 ath6kl_wmi_keepalive_reply_rx(struct wmi *wmi, u8 *datap, int len) argument
1274 ath6kl_wmi_scan_complete_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) argument
1287 ath6kl_wmi_neighbor_report_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) argument
1323 ath6kl_wmi_error_event_rx(struct wmi *wmi, u8 *datap, int len) argument
1347 ath6kl_wmi_stats_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) argument
1408 ath6kl_wmi_rssi_threshold_event_rx(struct wmi *wmi, u8 *datap, int len) argument
1504 ath6kl_wmi_cac_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) argument
1577 ath6kl_wmi_txe_notify_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) argument
1661 ath6kl_wmi_snr_threshold_event_rx(struct wmi *wmi, u8 *datap, int len) argument
1751 ath6kl_wmi_aplist_event_rx(struct wmi *wmi, u8 *datap, int len) argument
3333 ath6kl_wmi_get_pmkid_list_event_rx(struct wmi *wmi, u8 *datap, u32 len) argument
3352 ath6kl_wmi_addba_req_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) argument
3363 ath6kl_wmi_delba_req_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) argument
3473 ath6kl_wmi_pspoll_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) argument
3488 ath6kl_wmi_dtimexpiry_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) argument
3818 ath6kl_wmi_hb_challenge_resp_event(struct wmi *wmi, u8 *datap, int len) argument
3836 u8 *datap; local
3870 ath6kl_wmi_roam_tbl_event_rx(struct wmi *wmi, u8 *datap, int len) argument
3876 ath6kl_wmi_proc_events_vif(struct wmi *wmi, u16 if_idx, u16 cmd_id, u8 *datap, u32 len) argument
3966 u8 *datap; local
[all...]
/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/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/x86/kernel/
H A Dptrace.c734 unsigned long __user *datap = (unsigned long __user *)data; local
761 ret = put_user(tmp, datap);
785 datap);
792 datap);
799 datap);
806 datap);
813 datap) ? -EIO : 0;
819 datap) ? -EIO : 0;
1069 void __user *datap = compat_ptr(data); local
1077 ret = put_user(val, (__u32 __user *)datap);
1138 void __user *datap = compat_ptr(data); local
[all...]
/linux-master/lib/
H A Ddigsig.c79 uint8_t *p, *datap; local
107 datap = pkh->mpi;
111 unsigned int remaining = endp - datap;
112 pkey[i] = mpi_read_from_buffer(datap, &remaining);
117 datap += remaining;
/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);
/linux-master/arch/xtensa/kernel/
H A Dptrace.c415 long __user *datap)
442 if (copy_to_user(datap, user_data, sizeof(user_data)))
449 long __user *datap)
462 if (copy_from_user(user_data, datap, sizeof(user_data)))
501 void __user *datap = (void __user *) data; local
505 ret = ptrace_peekusr(child, addr, datap);
513 ret = ptrace_getregs(child, datap);
517 ret = ptrace_setregs(child, datap);
521 ret = ptrace_getxregs(child, datap);
525 ret = ptrace_setxregs(child, datap);
414 ptrace_gethbpregs(struct task_struct *child, long addr, long __user *datap) argument
448 ptrace_sethbpregs(struct task_struct *child, long addr, long __user *datap) argument
[all...]
/linux-master/arch/sh/kernel/
H A Dptrace_32.c341 unsigned long __user *datap = (unsigned long __user *)data; local
384 ret = put_user(tmp, datap);
417 datap);
422 datap);
428 datap);
433 datap);
440 datap);
445 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/tools/perf/util/
H A Dexpr.h46 struct expr_id_data **datap);
/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

Completed in 274 milliseconds

123