Issue with Ubuntu clang version 16.0.6 (15)

[neozeed]

I'm trying to build on a new Milk-V Jupiter board.

clang reports:

jsteve@milkv-jupiter:~/src/sse2rvv$ clang++ -v
Ubuntu clang version 16.0.6 (15)
Target: riscv64-unknown-linux-gnu
Thread model: posix
InstalledDir: /usr/bin
Found candidate GCC installation: /usr/bin/../lib/gcc/riscv64-linux-gnu/13
Selected GCC installation: /usr/bin/../lib/gcc/riscv64-linux-gnu/13

and the cpu type:

jsteve@milkv-jupiter:~/src/sse2rvv$ cat /proc/cpuinfo
processor       : 0
hart            : 0
model name      : Spacemit(R) X60
isa             : rv64imafdcv_sscofpmf_sstc_svpbmt_zicbom_zicboz_zicbop_zihintpause
mmu             : sv39
mvendorid       : 0x710
marchid         : 0x8000000058000001
mimpid          : 0x1000000049772200

The output from trying to do the test:

jsteve@milkv-jupiter:~/src/sse2rvv$ make test CXX=clang++
clang++ -o tests/common.o -static -Wall -Wcast-qual -I. -march=rv64gcv_zba  -c -MMD -MF tests/common.o.d tests/common.cpp
In file included from tests/common.cpp:1:
In file included from tests/common.h:5:
./sse2rvv.h:437:7: error: use of undeclared identifier '__riscv_vreinterpret_v_i32m1_b32'
      __riscv_vreinterpret_v_i32m1_b32(__riscv_vmv_s_x_i32m1(0xa, 4));
      ^
./sse2rvv.h:499:39: error: use of undeclared identifier '__RISCV_VXRM_RNU'
      __riscv_vaaddu_vv_u16m1(_a, _b, __RISCV_VXRM_RNU, 8));
                                      ^
./sse2rvv.h:506:38: error: use of undeclared identifier '__RISCV_VXRM_RNU'
      __riscv_vaaddu_vv_u8m1(_a, _b, __RISCV_VXRM_RNU, 16));
                                     ^
./sse2rvv.h:516:39: error: use of undeclared identifier '__RISCV_VXRM_RNU'
      __riscv_vaaddu_vv_u16m1(_a, _b, __RISCV_VXRM_RNU, 4));
                                      ^
./sse2rvv.h:523:38: error: use of undeclared identifier '__RISCV_VXRM_RNU'
      __riscv_vaaddu_vv_u8m1(_a, _b, __RISCV_VXRM_RNU, 8));
                                     ^
./sse2rvv.h:530:7: error: use of undeclared identifier '__riscv_vreinterpret_v_i8m1_b16'
      __riscv_vreinterpret_v_i8m1_b16(__riscv_vmv_s_x_i8m1(imm8, 8));
      ^
./sse2rvv.h:538:7: error: use of undeclared identifier '__riscv_vreinterpret_v_i8m1_b64'; did you mean '__riscv_vreinterpret_v_i8m1_i64m1'?
      __riscv_vreinterpret_v_i8m1_b64(__riscv_vmv_s_x_i8m1(imm8, 2));
      ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
      __riscv_vreinterpret_v_i8m1_i64m1
./sse2rvv.h:538:7: note: '__riscv_vreinterpret_v_i8m1_i64m1' declared here
./sse2rvv.h:537:13: error: cannot initialize a variable of type 'vbool64_t' (aka '__rvv_bool64_t') with an rvalue of type '__rvv_int64m1_t'
  vbool64_t _imm8 =
            ^
./sse2rvv.h:546:7: error: use of undeclared identifier '__riscv_vreinterpret_v_i8m1_b32'; did you mean '__riscv_vreinterpret_v_i8m1_i32m1'?
      __riscv_vreinterpret_v_i8m1_b32(__riscv_vmv_s_x_i8m1(imm8, 4));
      ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
      __riscv_vreinterpret_v_i8m1_i32m1
./sse2rvv.h:546:7: note: '__riscv_vreinterpret_v_i8m1_i32m1' declared here
./sse2rvv.h:545:13: error: cannot initialize a variable of type 'vbool32_t' (aka '__rvv_bool32_t') with an rvalue of type '__rvv_int32m1_t'
  vbool32_t _imm8 =
            ^
./sse2rvv.h:1384:55: error: use of undeclared identifier '__RISCV_FRM_RNE'
  vint32m1_t a_i32 = __riscv_vfcvt_x_f_v_i32m1_rm(_a, __RISCV_FRM_RNE, 1);
                                                      ^
./sse2rvv.h:1718:20: error: use of undeclared identifier '__riscv_vreinterpret_v_u8m1_b32'; did you mean '__riscv_vreinterpret_v_u8m1_u32m1'?
  vbool32_t mask = __riscv_vreinterpret_v_u8m1_b32(__riscv_vmv_s_x_u8m1(85, 2));
                   ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
                   __riscv_vreinterpret_v_u8m1_u32m1
./sse2rvv.h:1718:20: note: '__riscv_vreinterpret_v_u8m1_u32m1' declared here
./sse2rvv.h:1718:13: error: cannot initialize a variable of type 'vbool32_t' (aka '__rvv_bool32_t') with an rvalue of type '__rvv_uint32m1_t'
  vbool32_t mask = __riscv_vreinterpret_v_u8m1_b32(__riscv_vmv_s_x_u8m1(85, 2));
            ^      ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
./sse2rvv.h:1802:20: error: use of undeclared identifier '__riscv_vreinterpret_v_u8m1_b32'; did you mean '__riscv_vreinterpret_v_u8m1_u32m1'?
  vbool32_t mask = __riscv_vreinterpret_v_u8m1_b32(__riscv_vmv_s_x_u8m1(85, 2));
                   ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
                   __riscv_vreinterpret_v_u8m1_u32m1
./sse2rvv.h:1802:20: note: '__riscv_vreinterpret_v_u8m1_u32m1' declared here
./sse2rvv.h:1802:13: error: cannot initialize a variable of type 'vbool32_t' (aka '__rvv_bool32_t') with an rvalue of type '__rvv_uint32m1_t'
  vbool32_t mask = __riscv_vreinterpret_v_u8m1_b32(__riscv_vmv_s_x_u8m1(85, 2));
            ^      ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
./sse2rvv.h:1862:20: error: use of undeclared identifier '__riscv_vreinterpret_v_u8m1_b16'
  vbool16_t mask = __riscv_vreinterpret_v_u8m1_b16(
                   ^
./sse2rvv.h:1869:20: error: use of undeclared identifier '__riscv_vreinterpret_v_u8m1_b32'; did you mean '__riscv_vreinterpret_v_u8m1_u32m1'?
  vbool32_t mask = __riscv_vreinterpret_v_u8m1_b32(
                   ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
                   __riscv_vreinterpret_v_u8m1_u32m1
./sse2rvv.h:1869:20: note: '__riscv_vreinterpret_v_u8m1_u32m1' declared here
./sse2rvv.h:1869:13: error: cannot initialize a variable of type 'vbool32_t' (aka '__rvv_bool32_t') with an rvalue of type '__rvv_uint32m1_t'
  vbool32_t mask = __riscv_vreinterpret_v_u8m1_b32(
            ^      ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
./sse2rvv.h:1876:20: error: use of undeclared identifier '__riscv_vreinterpret_v_u8m1_b64'; did you mean '__riscv_vreinterpret_v_u8m1_u64m1'?
  vbool64_t mask = __riscv_vreinterpret_v_u8m1_b64(
                   ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
                   __riscv_vreinterpret_v_u8m1_u64m1
./sse2rvv.h:1876:20: note: '__riscv_vreinterpret_v_u8m1_u64m1' declared here
fatal error: too many errors emitted, stopping now [-ferror-limit=]
20 errors generated.
make: *** [Makefile:66: tests/common.o] Error 1
jsteve@milkv-jupiter:~/src/sse2rvv$

I guess the spec drifted?

[howjmay]

Hi @neozeed thank you for using the project.

I checked out the release note in clang-16.
https://releases.llvm.org/16.0.0/tools/clang/docs/ReleaseNotes.html#risc-v-support

An overall simplification of the RISC-V Vector intrinsics are done. The simplification is based on riscv-non-isa/rvv-intrinsic-doc#186.

Based on this, I guess they may not implement the reinterpret intrinsics.

I may need to take a deeper look. But the riscv header file is a little bit tricky. I will try to check anyway. If you have any information, please let me know.

[neozeed]

I wish I knew more. I thought this kind of thing has been abstracted away.

I wonder how the hackintosh folks did their sse2 emulation. Or was it sse3? I'm pretty sure Rosetta needed it for some reason.

[howjmay]

May I ask for more context. I may miss something, however these sound like different cases.
I think Rosetta converts x86 instructions into arm instructions. Therefore, with cross-compilation, we still can have the executable. However, the problem now is, clang-16 doesnt complete support rvv. So a newer version may help.