On Thu, Mar 2, 2023 at 7:27 PM Björn Töpel <bjorn@xxxxxxxxxx> wrote:
>
> Andy Chiu <andy.chiu@xxxxxxxxxx> writes:
>
> > diff --git a/arch/riscv/kernel/ptrace.c b/arch/riscv/kernel/ptrace.c
> > index 2ae8280ae475..3c0e01d7f8fb 100644
> > --- a/arch/riscv/kernel/ptrace.c
> > +++ b/arch/riscv/kernel/ptrace.c
> > @@ -83,6 +87,62 @@ static int riscv_fpr_set(struct task_struct *target,
> > }
> > #endif
> >
> > +#ifdef CONFIG_RISCV_ISA_V
> > +static int riscv_vr_get(struct task_struct *target,
> > + const struct user_regset *regset,
> > + struct membuf to)
> > +{
> > + struct __riscv_v_ext_state *vstate = &target->thread.vstate;
> > +
> > + if (!riscv_v_vstate_query(task_pt_regs(target)))
> > + return -EINVAL;
> > + /*
> > + * Ensure the vector registers have been saved to the memory before
> > + * copying them to membuf.
> > + */
> > + if (target == current)
> > + riscv_v_vstate_save(current, task_pt_regs(current));
> > +
> > + /* Copy vector header from vstate. */
> > + membuf_write(&to, vstate, offsetof(struct __riscv_v_ext_state, datap));
> > + membuf_zero(&to, sizeof(void *));
> > +#if __riscv_xlen == 32
> > + membuf_zero(&to, sizeof(__u32));
> > +#endif
>
> Remind me why the extra care is needed for 32b?
>
That is from the old version of the code and I agree we should remove
that. Hey Conor, does your Rb still hold after removing this #if,
#endif section?
>
> Björn
Andy
