diff options
| author | Chunyan Zhang <zhangchunyan@iscas.ac.cn> | 2025-11-17 21:19:24 -0700 |
|---|---|---|
| committer | Paul Walmsley <pjw@kernel.org> | 2025-11-19 09:19:28 -0700 |
| commit | 6fcce9f028fb75ce03e4221f5f4f652741d178c4 (patch) | |
| tree | e66452a3a4cebdcfd888546c77e9c2373a2e6d0c /lib/raid6/rvv.c | |
| parent | 724c69447975e1e0854082c324b6871c8e2214f8 (diff) | |
raid6: riscv: Prevent compiler from breaking inline vector assembly code
To prevent the compiler from breaking the inline vector assembly code,
this code must be built without compiler support for vector.
Signed-off-by: Chunyan Zhang <zhangchunyan@iscas.ac.cn>
Link: https://patch.msgid.link/20250718072711.3865118-4-zhangchunyan@iscas.ac.cn
[pjw@kernel.org: cleaned up commit message]
Signed-off-by: Paul Walmsley <pjw@kernel.org>
Diffstat (limited to 'lib/raid6/rvv.c')
| -rw-r--r-- | lib/raid6/rvv.c | 4 |
1 files changed, 4 insertions, 0 deletions
diff --git a/lib/raid6/rvv.c b/lib/raid6/rvv.c index 89da5fc247aa..015f3ee4da25 100644 --- a/lib/raid6/rvv.c +++ b/lib/raid6/rvv.c @@ -20,6 +20,10 @@ static int rvv_has_vector(void) return has_vector(); } +#ifdef __riscv_vector +#error "This code must be built without compiler support for vector" +#endif + static void raid6_rvv1_gen_syndrome_real(int disks, unsigned long bytes, void **ptrs) { u8 **dptr = (u8 **)ptrs; |