前一段時間遇到給D1下載程序觸發異常的問題。研究許久無果，多日后終得解決。

問題
使用全志提供的命令下載的方式，若在第一個線程啟動前不做停止操作（添加while(1),延時）等操作，使用該種方式下載會觸發異常。

使用全志PhoenixSuit工具下載不會觸發異常。

問題定位
最終問題出現定位在第一個線程啟動前。可惜水平有限，還是沒找到原因。

問題解決
經高人指點，發現mstatus中的vs位在第一個線程啟動前被修改。

于是在啟動第一個線程前，開始排查修改vs位的地方。

最終發現是在初始化線程的現場時被修改。

rt_uint8_t *rt_hw_stack_init(void *tentry,
void *parameter,
rt_uint8_t *stack_addr,
void *texit)
{
struct rt_hw_stack_frame *frame;
rt_uint8_t *stk;
int i;
extern int __global_pointer$;
stk = stack_addr + sizeof(rt_ubase_t);
stk = (rt_uint8_t *)RT_ALIGN_DOWN((rt_ubase_t)stk, REGBYTES);
stk -= sizeof(struct rt_hw_stack_frame);
frame = (struct rt_hw_stack_frame *)stk;
for (i = 0; i < sizeof(struct rt_hw_stack_frame) / sizeof(rt_ubase_t); i++)
{
((rt_ubase_t )frame)[i] = i;
}
frame->ra = (rt_ubase_t)texit;
frame->gp = (rt_ubase_t)&__global_pointer$;
frame->a0 = (rt_ubase_t)parameter;
frame->epc = (rt_ubase_t)tentry;
frame->x2 = (rt_ubase_t)stk;
/ force to supervisor mode(SPP=1) and set SPIE and SUM to 1 /
#ifdef ENABLE_FPU
frame->mstatus = MSTATUS_VS| MSTATUS_PUM | MSTATUS_FS | MSTATUS_MPP | MSTATUS_MPIE; / enable FPU */
#else
frame->mstatus = MSTATUS_PUM | MSTATUS_MPP | MSTATUS_MPIE;
#endif
return stk;
}
上述代碼修改前，下載會觸發異常：

frame- >mstatus = MSTATUS_PUM | MSTATUS_FS | MSTATUS_MPP | MSTATUS_MPIE;    /* enable FPU */

修改后，下載正常：

frame- >mstatus = MSTATUS_VS| MSTATUS_PUM | MSTATUS_FS | MSTATUS_MPP | MSTATUS_MPIE;    /* enable FPU */

為什么這么改？請看下文：

事情到這就清晰了，是因為沒有初始化向量指令控制位VS.

回到最初的問題：

下載主要的操作就是數據拷貝，使用向量指令拷貝會大大加速下載速度，所以全志的下載算法會使用向量指令去拷貝，這里沒有初始化VS,當然會觸發異常了。

到這還有個疑問：

mstatus的vs在用戶程序中修改的，這里按道理已經在用戶程序了，整么還在下載，這個問題就不得而知了，你知道嗎,反正我不知道

一番操作過后，看看這個向量指令到底是個啥吧：

向量指令
向量指令：單條指令操作多個數據，并行

使用場景：數據拷貝 用并行方式代替循環的方式

向量指令使用舉例：
一段上下文切換中的代碼：

#ifdef __riscv_vector
addi sp, sp, -(20+20)
csrr t0, vl // 記錄 矢量寄存器 能 處理的 數據 個數
sd t0, (0 +0 )(sp) // 備份
csrr t0, vtype // 描述 矢量寄存器 數據 類型
sd t0, (4 +4 )(sp) // 備份
csrr t0, vstart // 向量 起始 索引 向量指令 執行 第一個元素 的 索引
sd t0, (8 +8 )(sp) // 備份
csrr t0, vxsat // 描述 運算 結果 是否 飽和
sd t0, (12 +12 )(sp) // 備份
csrr t0, vxrm // 舍入 模式 類似四舍五入的(略) 那種
sd t0, (16 +16 )(sp) // 備份
addi sp, sp, -(256+256)
vsetvli zero, zero, e8, m8 // 設置 數據寬度8（1字節） 8個向量寄存器為一組
vsb.v v0, (sp) //存儲V0 ~ V7 矢量寄存器數據至 內存 存儲數量 (128:矢量寄存器寬度 / 8:數據寬度) * 8:矢量寄存器組中的矢量寄存器的個數
addi sp, sp, 128//
vsb.v v8, (sp) // 存儲V8 ~ V15
addi sp, sp, 128
vsb.v v16, (sp)// 存儲V16 ~ V23
addi sp, sp, 128
vsb.v v24, (sp)// 存儲V24 ~ V31
addi sp, sp, -(256+256-128)
#endif
la t2, do_irq// 處理中斷
jalr t2
#ifdef __riscv_vector
vsetvli zero, zero, e8, m8 // 采用與之前同樣的配置方式
vlb.v v0, (sp)
addi sp, sp, 128//拷貝V0 ~ V7 內存 至矢量寄存器數 拷貝數量 (128:矢量寄存器寬度 / 8:數據寬度) * 8:矢量寄存器組中的矢量寄存器的個數
vlb.v v8, (sp)
addi sp, sp, 128//拷貝V8 ~ V15
vlb.v v16, (sp)
addi sp, sp, 128//拷貝V16 ~ V23
vlb.v v24, (sp)
addi sp, sp, 128//拷貝V24 ~ V31
lwu t0, (0 +0)(sp)// 加載 vl
lwu t1, (4 +4)(sp)// 加載 vtype
lwu t2, (8 +8)(sp)// 加載 vstart
vsetvl zero, t0, t1 // 重新設置 vl vtype
csrw vstart, t2// 加載 vstart
lwu t2, (12 +12)(sp)
csrw vxsat, t2 // 加載 vxsat
lwu t2, (16 +16)(sp)
csrw vxrm, t2 // 加載 vxrm
addi sp, sp, (20+20)
#endif
RISC-V小學生，不住之處請多多指教.