riscv/kernel/ptrace.c

92 	struct __riscv_v_ext_state *vstate = &target->thread.vstate;
104 		riscv_v_vstate_save(&current->thread.vstate, task_pt_regs(current));
108 	ptrace_vstate.vstart = vstate->vstart;
109 	ptrace_vstate.vl = vstate->vl;
110 	ptrace_vstate.vtype = vstate->vtype;
111 	ptrace_vstate.vcsr = vstate->vcsr;
112 	ptrace_vstate.vlenb = vstate->vlenb;
114 	/* Copy vector header from vstate. */
117 	/* Copy all the vector registers from vstate. */
118 	return membuf_write(&to, vstate->datap, riscv_v_vsize);
127 	struct __riscv_v_ext_state *vstate = &target->thread.vstate;
133 	/* Copy rest of the vstate except datap */
139 	if (vstate->vlenb != ptrace_vstate.vlenb)
142 	vstate->vstart = ptrace_vstate.vstart;
143 	vstate->vl = ptrace_vstate.vl;
144 	vstate->vtype = ptrace_vstate.vtype;
145 	vstate->vcsr = ptrace_vstate.vcsr;
149 	ret = user_regset_copyin(&pos, &count, &kbuf, &ubuf, vstate->datap,