Home
last modified time | relevance | path

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

1234

/openbmc/linux/tools/testing/selftests/riscv/vector/
H A Dv_initval_nolibc.c26 char *datap, *tmp; in main() local
28 datap = malloc(MAX_VSIZE); in main()
29 if (!datap) { in main()
34 tmp = datap; in main()
47 : "=&r" (vl), "=r" (tmp) : "r" (datap) : "memory"); in main()
51 if (datap[0] != 0x00 && datap[0] != 0xff) { in main()
53 dump(datap, vl * 4); in main()
58 if (datap[i] != datap[0]) { in main()
60 dump(datap, vl * 4); in main()
65 free(datap); in main()
/openbmc/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 …]
/openbmc/linux/arch/riscv/kvm/
H A Dvcpu_vector.c27 WARN_ON(!cntx->vector.datap); in kvm_riscv_vcpu_vector_reset()
28 memset(cntx->vector.datap, 0, riscv_v_vsize); in kvm_riscv_vcpu_vector_reset()
76 cntx->vector.datap = kmalloc(riscv_v_vsize, GFP_KERNEL); in kvm_riscv_vcpu_alloc_vector_context()
77 if (!cntx->vector.datap) in kvm_riscv_vcpu_alloc_vector_context()
80 vcpu->arch.host_context.vector.datap = kzalloc(riscv_v_vsize, GFP_KERNEL); in kvm_riscv_vcpu_alloc_vector_context()
81 if (!vcpu->arch.host_context.vector.datap) in kvm_riscv_vcpu_alloc_vector_context()
89 kfree(vcpu->arch.guest_reset_context.vector.datap); in kvm_riscv_vcpu_free_vector_context()
90 kfree(vcpu->arch.host_context.vector.datap); in kvm_riscv_vcpu_free_vector_context()
118 case KVM_REG_RISCV_VECTOR_CSR_REG(datap): in kvm_riscv_vcpu_vreg_addr()
125 *reg_addr = cntx->vector.datap + in kvm_riscv_vcpu_vreg_addr()
/openbmc/linux/drivers/base/
H A Dplatform-msi.c146 struct platform_msi_priv_data *datap; in platform_msi_alloc_priv_data() local
171 datap = kzalloc(sizeof(*datap), GFP_KERNEL); in platform_msi_alloc_priv_data()
172 if (!datap) in platform_msi_alloc_priv_data()
175 datap->devid = ida_simple_get(&platform_msi_devid_ida, in platform_msi_alloc_priv_data()
177 if (datap->devid < 0) { in platform_msi_alloc_priv_data()
178 err = datap->devid; in platform_msi_alloc_priv_data()
179 kfree(datap); in platform_msi_alloc_priv_data()
183 datap->write_msg = write_msi_msg; in platform_msi_alloc_priv_data()
184 datap->dev = dev; in platform_msi_alloc_priv_data()
185 dev->msi.data->platform_data = datap; in platform_msi_alloc_priv_data()
/openbmc/linux/arch/riscv/kernel/
H A Dsignal.c77 void __user *datap; in save_v_state() local
83 /* Point datap right after the end of __sc_riscv_v_state */ in save_v_state()
84 datap = state + 1; in save_v_state()
86 /* datap is designed to be 16 byte aligned for better performance */ in save_v_state()
87 WARN_ON(unlikely(!IS_ALIGNED((unsigned long)datap, 16))); in save_v_state()
90 /* Copy everything of vstate but datap. */ in save_v_state()
92 offsetof(struct __riscv_v_ext_state, datap)); in save_v_state()
93 /* Copy the pointer datap itself. */ in save_v_state()
94 err |= __put_user(datap, &state->v_state.datap); in save_v_state()
117 void __user *datap; __restore_v_state() local
[all...]
H A Dvector.c85 void *datap; in riscv_v_thread_zalloc() local
87 datap = kzalloc(riscv_v_vsize, GFP_KERNEL); in riscv_v_thread_zalloc()
88 if (!datap) in riscv_v_thread_zalloc()
91 current->thread.vstate.datap = datap; in riscv_v_thread_zalloc()
93 datap)); in riscv_v_thread_zalloc()
158 WARN_ON(current->thread.vstate.datap); in riscv_v_first_use_handler()
/openbmc/linux/arch/m68k/kernel/
H A Dptrace.c168 unsigned long __user *datap = (unsigned long __user *) data; in arch_ptrace() local
196 ret = put_user(tmp, datap); in arch_ptrace()
228 ret = put_user(tmp, datap); in arch_ptrace()
231 datap++; in arch_ptrace()
237 ret = get_user(tmp, datap); in arch_ptrace()
245 datap++; in arch_ptrace()
250 if (copy_to_user(datap, &child->thread.fp, in arch_ptrace()
256 if (copy_from_user(&child->thread.fp, datap, in arch_ptrace()
262 ret = put_user(task_thread_info(child)->tp_value, datap); in arch_ptrace()
/openbmc/linux/arch/riscv/include/asm/
H A Dvector.h92 void *datap) in __riscv_v_vstate_save() argument
110 : "=&r" (vl) : "r" (datap) : "memory"); in __riscv_v_vstate_save()
115 void *datap) in __riscv_v_vstate_restore() argument
132 : "=&r" (vl) : "r" (datap) : "memory"); in __riscv_v_vstate_restore()
171 __riscv_v_vstate_save(vstate, vstate->datap); in riscv_v_vstate_save()
182 __riscv_v_vstate_restore(vstate, vstate->datap); in riscv_v_vstate_restore()
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()
/openbmc/linux/arch/arm64/kvm/
H A Dmmio.c15 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()
/openbmc/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()
/openbmc/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 …]
/openbmc/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 …]
/openbmc/u-boot/lib/efi/
H A Defi_info.c13 int efi_info_get(enum efi_entry_t type, void **datap, int *sizep) in efi_info_get() argument
32 *datap = map_sysmem(entry->addr, entry->size); in efi_info_get()
34 *datap = entry + 1; in efi_info_get()
/openbmc/u-boot/cmd/
H A Dsetexpr.c134 char *datap = data; in regex_sub() local
183 res = slre_match(&slre, datap, len, caps); in regex_sub()
270 datap = substitute(datap, &len, SLRE_BUFSZ, in regex_sub()
274 if (datap == NULL) in regex_sub()
277 debug("## REMAINDER: %s\n", datap); in regex_sub()
/openbmc/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()
/openbmc/linux/lib/
H A Ddigsig.c79 uint8_t *p, *datap; in digsig_verify_rsa() local
107 datap = pkh->mpi; in digsig_verify_rsa()
111 unsigned int remaining = endp - datap; in digsig_verify_rsa()
112 pkey[i] = mpi_read_from_buffer(datap, &remaining); in digsig_verify_rsa()
117 datap += remaining; in digsig_verify_rsa()
/openbmc/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 …]
/openbmc/linux/arch/x86/um/
H A Dptrace_32.c260 void __user *datap = (void __user *) data; in subarch_ptrace() local
263 ret = get_fpregs(datap, child); in subarch_ptrace()
266 ret = set_fpregs(datap, child); in subarch_ptrace()
269 ret = get_fpxregs(datap, child); in subarch_ptrace()
272 ret = set_fpxregs(datap, child); in subarch_ptrace()
/openbmc/qemu/tests/unit/
H A Dtest-visitor-serialization.c279 void (*serialize)(void *native_in, void **datap,
281 void (*deserialize)(void **native_out, void *datap,
283 void (*cleanup)(void *datap);
925 static void qmp_serialize(void *native_in, void **datap, in qmp_serialize() argument
932 *datap = d; in qmp_serialize()
935 static void qmp_deserialize(void **native_out, void *datap, in qmp_deserialize() argument
938 QmpSerializeData *d = datap; in qmp_deserialize()
954 static void qmp_cleanup(void *datap) in qmp_cleanup() argument
956 QmpSerializeData *d = datap; in qmp_cleanup()
969 static void string_serialize(void *native_in, void **datap, in string_serialize() argument
[all …]
/openbmc/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);
/openbmc/linux/arch/sh/lib/
H A Dio.c14 void __raw_readsl(const 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()

1234