VLEN是硬件寄存器总位宽，vscale是LLVM中VLEN/64的整数缩放因子；vscale必须为正整数，故VLEN须为64整数倍，当前LLVM仅支持ELEN=32或64，不支持VLEN=192等非64倍数值。
VLEN 是硬件决定的寄存器总位宽，vscale 是 LLVM 编译器用来建模 VLEN 可变性的整数缩放因子；二者不是等价替换，而是 vscale = VLEN / 64 的硬编码映射关系。
vscale 被固定为 VLEN / 64，不支持任意 VLEN
LLVM 当前（截至 2026 年）只承认 ELEN=32 或 ELEN=64，因此 vscale 被定义为 VLEN / 64（见 RISCV::RVVBitsPerBlock）。这意味着：
-
VLEN=64→vscale=1（最小合法值） -
VLEN=128→vscale=2 -
VLEN=256→vscale=4 -
VLEN=32不被支持——因为会推出vscale=0.5，而 vscale 必须是正整数
你写的 <vscale x i32></vscale> 类型，在 VLEN=256 的硬件上实际展开为 8 个 i32 元素（vscale=4 × 2 = 8），而不是固定为 2 个。
vsetvli 返回的 vl 值由 vscale 和 LMUL/SEW 共同决定
vsetvli 指令不直接读取 vscale，但它隐含依赖 vscale 所代表的 VLEN。例如：
- 调用
__riscv_vsetvl_e32m4(100)时，LLVM 生成的指令会基于当前硬件的 VLEN 计算VLMAX = (VLEN × LMUL) / SEW = (VLEN × 4) / 32 - 若 VLEN=128，则
VLMAX = (128 × 4) / 32 = 16，所以vl最大为 16 - 若 VLEN=512，则
VLMAX = (512 × 4) / 32 = 64，vl最大为 64
也就是说，同一份 C 代码调用同一个 intrinsic，返回的 vl 值会随硬件 VLEN 不同而变化——这正是 vscale 抽象要支撑的“向量长度无关”行为。
写 IR 或手写汇编时，vscale 是类型系统里的第一公民，VLEN 则完全不可见
在 LLVM IR 中你只能看到 <vscale x n t></vscale>，看不到 VLEN。例如：
define <vscale x 4 x float> @foo(<vscale x 4 x float> %a) {
%b = fadd <vscale x 4 x float> %a, %a
ret <vscale x 4 x float> %b
}
这段 IR 在不同 VLEN 硬件上会被后端翻译成不同宽度的实际向量指令（如 v0-v3 组合或 v0-v7 组合），但 IR 本身不感知 VLEN。编译器靠 vscale 推导寄存器需求、对齐约束和内存访问模式——比如 <vscale x i8></vscale> 在 VLEN=128 时占 128 位（16 字节），在 VLEN=512 时占 640 位（80 字节），对齐要求完全不同。
容易忽略的是：vscale 的整数性导致 VLEN 必须是 64 的整数倍；而真实硬件可能实现 VLEN=192 或 VLEN=384（比如某些定制核），这类平台目前无法被 LLVM RVV 后端原生支持——你得手动绕过 vscale 抽象，用汇编或 vendor-specific intrinsics 补位。
