Lines Matching refs:datap
77 void __user *datap;
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);
98 /* Copy the whole vector content to user space datap. */
99 err |= __copy_to_user(datap, current->thread.vstate.datap, riscv_v_vsize);
120 void __user *datap;
129 /* Copy everything of __sc_riscv_v_state except datap. */
131 offsetof(struct __riscv_v_ext_state, datap));
135 /* Copy the pointer datap itself. */
136 err = __get_user(datap, &state->v_state.datap);
140 * Copy the whole vector content from user space datap. Use
143 return copy_from_user(current->thread.vstate.datap, datap, riscv_v_vsize);