Firmware/opensbi
8
0
Fork 0
forked from Mirrors/opensbi
Code Pull Requests Activity

Makefile: Don't enable V-extension using -march option

Browse Source 
Enabling V-extension using -march option causes OpenSBI boot-time
hang with LLVM compiler.

As a work-around, don't enable V-extension using -march option and
instead use a custom OpenSBI specific define inform availability of
V-extension to lib/sbi/sbi_trap_v_ldst.c.

Fixes: c2acc5e5b0 ("lib: sbi_misaligned_ldst: Add handling of vector load/store")
Signed-off-by: Anup Patel <apatel@ventanamicro.com>
Reviewed-by: Samuel Holland <samuel.holland@sifive.com>
This commit is contained in:
Anup Patel
2024-12-09 20:06:18 +05:30
committed by Anup Patel
parent 74c6ea014d
commit 5545602f77
2 changed files with 7 additions and 6 deletions
Download Patch File Download Diff File Expand all files Collapse all files

5
lib/sbi/sbi_trap_v_ldst.c
View File

@@ -17,7 +17,8 @@
#include <sbi/sbi_unpriv.h>
#include <sbi/sbi_trap.h>
#ifdef __riscv_vector
#ifdef OPENSBI_CC_SUPPORT_VECTOR
#define VLEN_MAX 65536
static inline void set_vreg(ulong vlenb, ulong which,
@@ -340,4 +341,4 @@ int sbi_misaligned_v_st_emulator(int wlen, union sbi_ldst_data in_val,
{
return 0;
}
#endif /* __riscv_vector */
#endif /* OPENSBI_CC_SUPPORT_VECTOR */