RISC-V: Add ptrace support for vectors
authorAndy Chiu <andy.chiu@sifive.com>
Fri, 25 Aug 2023 05:02:46 +0000 (05:02 +0000)
committerPalmer Dabbelt <palmer@rivosinc.com>
Fri, 1 Sep 2023 20:05:38 +0000 (13:05 -0700)
commit9300f00439743c4a34d735e1a27118eb68a1504e
tree302e170bdb865dca73b5646cb23b4aac3809af9b
parentc35f3aa34509085bfc9800c86bc9998f8954933d
RISC-V: Add ptrace support for vectors

This patch add back the ptrace support with the following fix:
 - Define NT_RISCV_CSR and re-number NT_RISCV_VECTOR to prevent
   conflicting with gdb's NT_RISCV_CSR.
 - Use struct __riscv_v_regset_state to handle ptrace requests

Since gdb does not directly include the note description header in
Linux and has already defined NT_RISCV_CSR as 0x900, we decide to
sync with gdb and renumber NT_RISCV_VECTOR to solve and prevent future
conflicts.

Fixes: 0c59922c769a ("riscv: Add ptrace vector support")
Signed-off-by: Andy Chiu <andy.chiu@sifive.com>
Link: https://lore.kernel.org/r/20230825050248.32681-1-andy.chiu@sifive.com
[Palmer: Drop the unused "size" variable in riscv_vr_set().]
Signed-off-by: Palmer Dabbelt <palmer@rivosinc.com>
arch/riscv/include/uapi/asm/ptrace.h
arch/riscv/kernel/ptrace.c
include/uapi/linux/elf.h