__riscv_v_vstate_save
__riscv_v_vstate_save(&context->vector, context->vector.datap);
__riscv_v_vstate_save(vstate, vstate->datap);
__riscv_v_vstate_save(&prev->thread.kernel_vstate,
__riscv_v_vstate_save(kvstate, kvstate->datap);
__riscv_v_vstate_save(uvstate, uvstate->datap);