Home
last modified time | relevance | path

Searched refs:datap (Results 1 – 25 of 62) sorted by relevance

123

/linux/drivers/net/wireless/ath/ath6kl/
H A Dwmi.c166 u8 *datap; in ath6kl_wmi_dix_2_dot3() local
188 datap = skb->data; in ath6kl_wmi_dix_2_dot3()
192 memcpy(datap, eth_hdr, sizeof(*eth_hdr)); in ath6kl_wmi_dix_2_dot3()
194 llc_hdr = (struct ath6kl_llc_snap_hdr *)(datap + sizeof(*eth_hdr)); in ath6kl_wmi_dix_2_dot3()
310 u8 *datap; in ath6kl_wmi_implicit_create_pstream() local
315 datap = skb->data; in ath6kl_wmi_implicit_create_pstream()
316 data_hdr = (struct wmi_data_hdr *) datap; in ath6kl_wmi_implicit_create_pstream()
327 llc_hdr = (struct ath6kl_llc_snap_hdr *)(datap + in ath6kl_wmi_implicit_create_pstream()
394 u8 *datap; in ath6kl_wmi_dot11_hdr_remove() local
400 datap = skb->data; in ath6kl_wmi_dot11_hdr_remove()
[all …]
H A Dtxrx.c48 u8 *datap; in ath6kl_ibss_map_epid() local
51 datap = skb->data; in ath6kl_ibss_map_epid()
52 eth_hdr = (struct ethhdr *) (datap + sizeof(struct wmi_data_hdr)); in ath6kl_ibss_map_epid()
109 struct ethhdr *datap = (struct ethhdr *) skb->data; in ath6kl_process_uapsdq() local
133 ether_type = be16_to_cpu(datap->h_proto); in ath6kl_process_uapsdq()
136 ip_hdr = (u8 *)(datap + 1); in ath6kl_process_uapsdq()
140 (datap + 1); in ath6kl_process_uapsdq()
212 struct ethhdr *datap = (struct ethhdr *) skb->data; in ath6kl_powersave_ap() local
217 if (is_multicast_ether_addr(datap->h_dest)) { in ath6kl_powersave_ap()
265 conn = ath6kl_find_sta(vif, datap->h_dest); in ath6kl_powersave_ap()
[all …]
/linux/arch/m68k/kernel/
H A Dptrace.c170 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()
/linux/arch/riscv/kernel/
H A Dsignal.c76 void __user *datap; in save_v_state() local
87 datap = state + 1; in save_v_state()
90 WARN_ON(!IS_ALIGNED((unsigned long)datap, 16)); in save_v_state()
98 offsetof(struct __riscv_v_ext_state, datap)); in save_v_state()
100 err |= __put_user((__force void *)datap, &state->v_state.datap); in save_v_state()
102 err |= __copy_to_user(datap, current->thread.vstate.datap, riscv_v_vsize); in save_v_state()
119 void __user *datap; in __restore_v_state() local
130 offsetof(struct __riscv_v_ext_state, datap)); in __restore_v_state()
135 err = __get_user(datap, &state->v_state.datap); in __restore_v_state()
142 return copy_from_user(current->thread.vstate.datap, datap, riscv_v_vsize); in __restore_v_state()
H A Dkernel_mode_vector.c129 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()
/linux/arch/riscv/include/asm/
H A Dvector.h197 void *datap) in __riscv_v_vstate_save() argument
214 : : "r" (datap) : "memory", "t0", "t4"); in __riscv_v_vstate_save()
228 : "=&r" (vl) : "r" (datap) : "memory"); in __riscv_v_vstate_save()
234 void *datap) in __riscv_v_vstate_restore() argument
250 : : "r" (datap) : "memory", "t0", "t4"); in __riscv_v_vstate_restore()
264 : "=&r" (vl) : "r" (datap) : "memory"); in __riscv_v_vstate_restore()
310 __riscv_v_vstate_save(vstate, vstate->datap); in riscv_v_vstate_save()
319 __riscv_v_vstate_restore(vstate, vstate->datap); in riscv_v_vstate_restore()
382 prev->thread.kernel_vstate.datap); in __switch_to_vector()
H A Dkvm_vcpu_vector.h21 __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()
/linux/arch/x86/kernel/
H A Dptrace.c734 unsigned long __user *datap = (unsigned long __user *)data; in arch_ptrace() local
761 ret = put_user(tmp, datap); in arch_ptrace()
785 datap); in arch_ptrace()
792 datap); in arch_ptrace()
799 datap); in arch_ptrace()
806 datap); in arch_ptrace()
813 datap) ? -EIO : 0; in arch_ptrace()
819 datap) ? -EIO : 0; in arch_ptrace()
1069 void __user *datap = compat_ptr(data); in ia32_arch_ptrace() local
1077 ret = put_user(val, (__u32 __user *)datap); in ia32_arch_ptrace()
[all …]
/linux/tools/virtio/ringtest/
H A Dptr_ring.c128 int add_inbuf(unsigned len, void *buf, void *datap) in add_inbuf() argument
149 void *datap; in get_buf() local
152 datap = NULL; in get_buf()
154 datap = "Buffer\n"; in get_buf()
158 return datap; in get_buf()
H A Dring.c112 int add_inbuf(unsigned len, void *buf, void *datap) in add_inbuf() argument
135 data[index].data = datap; in add_inbuf()
147 void *datap; in get_buf() local
155 datap = data[index].data; in get_buf()
161 return datap; in get_buf()
H A Dvirtio_ring_0_9.c99 int add_inbuf(unsigned len, void *buf, void *datap) in add_inbuf() argument
130 data[head].data = datap; in add_inbuf()
156 void *datap; in get_buf() local
185 datap = data[index].data; in get_buf()
194 return datap; in get_buf()
/linux/arch/xtensa/kernel/
H A Dptrace.c415 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
462 if (copy_from_user(user_data, datap, sizeof(user_data))) in ptrace_sethbpregs()
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()
[all …]
/linux/arch/x86/um/
H A Dptrace_32.c176 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()
H A Dptrace_64.c196 void __user *datap = (void __user *) data; in subarch_ptrace() local
203 datap); in subarch_ptrace()
208 datap); in subarch_ptrace()
/linux/arch/sh/kernel/
H A Dptrace_32.c341 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()
/linux/lib/
H A Ddigsig.c75 uint8_t *p, *datap; in digsig_verify_rsa() local
103 datap = pkh->mpi; in digsig_verify_rsa()
107 unsigned int remaining = endp - datap; in digsig_verify_rsa()
108 pkey[i] = mpi_read_from_buffer(datap, &remaining); in digsig_verify_rsa()
113 datap += remaining; in digsig_verify_rsa()
/linux/arch/arm/kernel/
H A Dptrace.c729 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 …]
/linux/Documentation/translations/zh_CN/core-api/
H A Dthis_cpu_ops.rst251 DEFINE_PER_CPU(struct data, datap);
253 struct data *p = per_cpu_ptr(&datap, cpu);
257 您还可以执行以下操作以将datap偏移量转换为地址::
259 struct data *p = this_cpu_ptr(&datap);
/linux/arch/sh/lib/
H A Dio.c14 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()
/linux/drivers/net/usb/
H A Dsierra_net.c231 static const u8 *save16bit(struct param *p, const u8 *datap) in save16bit() argument
234 p->word = get_unaligned_be16(datap); in save16bit()
235 return datap + sizeof(p->word); in save16bit()
238 static const u8 *save8bit(struct param *p, const u8 *datap) in save8bit() argument
241 p->byte = *datap; in save8bit()
242 return datap + sizeof(p->byte); in save8bit()
625 static int sierra_net_get_fw_attr(struct usbnet *dev, u16 *datap) in sierra_net_get_fw_attr() argument
643 *datap = le16_to_cpu(attrdata); in sierra_net_get_fw_attr()
/linux/tools/testing/selftests/arm64/signal/testcases/
H A Dtestcases.c23 if (extra->datap & 0x0fUL) in validate_extra_context()
27 else if (extra->datap != (uint64_t)term + 0x10UL) in validate_extra_context()
32 *extra_data = (void *)extra->datap; in validate_extra_context()
/linux/security/integrity/ima/
H A Dima_fs.c289 char *datap;
296 datap = path; in ima_read_policy()
297 strsep(&datap, "\n"); in ima_read_policy()
308 datap = data; in ima_read_policy()
309 while (size > 0 && (p = strsep(&datap, "\n"))) { in ima_read_policy()
295 char *datap; ima_read_policy() local
/linux/arch/parisc/kernel/
H A Dptrace.c125 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()
/linux/tools/perf/util/
H A Dexpr.c243 struct expr_id_data **datap) in expr__resolve_id() argument
247 if (expr__get_id(ctx, id, datap) || !*datap) { in expr__resolve_id()
252 data = *datap; in expr__resolve_id()
/linux/security/selinux/ss/
H A Dpolicydb.c323 static int (*const destroy_f[SYM_NUM])(void *key, void *datum, void *datap) = {
552 static int common_index(void *key, void *datum, void *datap) in common_index() argument
558 p = datap; in common_index()
567 static int class_index(void *key, void *datum, void *datap) in class_index() argument
573 p = datap; in class_index()
582 static int role_index(void *key, void *datum, void *datap) in role_index() argument
588 p = datap; in role_index()
598 static int type_index(void *key, void *datum, void *datap) in type_index() argument
604 p = datap; in type_index()
617 static int user_index(void *key, void *datum, void *datap) in user_index() argument
[all …]

123