search

CHIP-SPV / chipStar

chipStar is a tool for compiling and running HIP/CUDA on SPIR-V via OpenCL or Level Zero APIs.
Other
219 stars 32 forks source link

error: call to '__shfl' is ambiguous #797

Open pvelesko opened 6 months ago

pvelesko commented 6 months ago

Error in #796 

[build] FAILED: catch/catch_tests/unit/kernel/CMakeFiles/KernelTest.dir/hipShflTests.cc.o 
[build] /space/pvelesko/chipStar/hip-tests-update/build/bin/hipcc  -I/space/pvelesko/chipStar/hip-tests-update/CHIP -I/space/pvelesko/chipStar/hip-tests-update/PUBLIC -I/usr/include/level_zero -I/space/pvelesko/chipStar/hip-tests-update/hip-tests/catch/external/Catch2 -I/space/pvelesko/chipStar/hip-tests-update/hip-tests/catch/./include -I/space/pvelesko/chipStar/hip-tests-update/hip-tests/catch/./kernels -I/space/pvelesko/chipStar/hip-tests-update/build/include -I/space/pvelesko/chipStar/hip-tests-update/hip-tests/catch/external/picojson -I/space/pvelesko/chipStar/hip-tests-update/build/catch -Wno-duplicate-decl-specifier -Wno-tautological-constant-compare  -Wno-c++20-extensions -Wno-unused-result -Wno-delete-abstract-non-virtual-dtor -Wno-deprecated-declarations -Wunused-command-line-argument --std=c++17 -g -fPIE -Wno-format-extra-args -mf16c -Wall -O1 -std=c++17 -MD -MT catch/catch_tests/unit/kernel/CMakeFiles/KernelTest.dir/hipShflTests.cc.o -MF catch/catch_tests/unit/kernel/CMakeFiles/KernelTest.dir/hipShflTests.cc.o.d -o catch/catch_tests/unit/kernel/CMakeFiles/KernelTest.dir/hipShflTests.cc.o -c /space/pvelesko/chipStar/hip-tests-update/hip-tests/catch/unit/kernel/hipShflTests.cc
[build] /space/pvelesko/chipStar/hip-tests-update/hip-tests/catch/unit/kernel/hipShflTests.cc:38:58: error: call to '__shfl' is ambiguous
[build]    38 |     for (int j = 0; j < width; j++) out[i * width + j] = __shfl(val, j * width + i);
[build]       |                                                          ^~~~~~
[build] /space/pvelesko/chipStar/hip-tests-update/hip-tests/catch/unit/kernel/hipShflTests.cc:125:22: note: in instantiation of function template specialization 'matrixTranspose<__half>' requested here
[build]   125 |   hipLaunchKernelGGL(matrixTranspose<T>, dim3(1), dim3(THREADS_PER_BLOCK_X * THREADS_PER_BLOCK_Y),
[build]       |                      ^
[build] /space/pvelesko/chipStar/hip-tests-update/hip-tests/catch/unit/kernel/hipShflTests.cc:173:36: note: in instantiation of function template specialization 'runTest<__half>' requested here
[build]   173 |   SECTION("run test for __half") { runTest<__half>(); }
[build]       |                                    ^
[build] /space/pvelesko/chipStar/hip-tests-update/include/hip/devicelib/sync_and_util.hh:130:1: note: candidate function
[build]   130 | DECL_SHFL_OPS(int);
[build]       | ^
[build] /space/pvelesko/chipStar/hip-tests-update/include/hip/devicelib/sync_and_util.hh:121:27: note: expanded from macro 'DECL_SHFL_OPS'
[build]   121 |   extern __device__ TYPE_ __shfl(TYPE_ var, int srcLane,                       \
[build]       |                           ^
[build] /space/pvelesko/chipStar/hip-tests-update/include/hip/devicelib/sync_and_util.hh:131:1: note: candidate function
[build]   131 | DECL_SHFL_OPS(unsigned int);
[build]       | ^
[build] /space/pvelesko/chipStar/hip-tests-update/include/hip/devicelib/sync_and_util.hh:121:27: note: expanded from macro 'DECL_SHFL_OPS'
[build]   121 |   extern __device__ TYPE_ __shfl(TYPE_ var, int srcLane,                       \
[build]       |                           ^
[build] /space/pvelesko/chipStar/hip-tests-update/include/hip/devicelib/sync_and_util.hh:132:1: note: candidate function
[build]   132 | DECL_SHFL_OPS(long);
[build]       | ^
[build] /space/pvelesko/chipStar/hip-tests-update/include/hip/devicelib/sync_and_util.hh:121:27: note: expanded from macro 'DECL_SHFL_OPS'
[build]   121 |   extern __device__ TYPE_ __shfl(TYPE_ var, int srcLane,                       \
[build]       |                           ^
[build] /space/pvelesko/chipStar/hip-tests-update/include/hip/devicelib/sync_and_util.hh:133:1: note: candidate function
[build]   133 | DECL_SHFL_OPS(unsigned long);
[build]       | ^
[build] /space/pvelesko/chipStar/hip-tests-update/include/hip/devicelib/sync_and_util.hh:121:27: note: expanded from macro 'DECL_SHFL_OPS'
[build]   121 |   extern __device__ TYPE_ __shfl(TYPE_ var, int srcLane,                       \
[build]       |                           ^
[build] /space/pvelesko/chipStar/hip-tests-update/include/hip/devicelib/sync_and_util.hh:134:1: note: candidate function
[build]   134 | DECL_SHFL_OPS(float);
[build]       | ^
[build] /space/pvelesko/chipStar/hip-tests-update/include/hip/devicelib/sync_and_util.hh:121:27: note: expanded from macro 'DECL_SHFL_OPS'
[build]   121 |   extern __device__ TYPE_ __shfl(TYPE_ var, int srcLane,                       \
[build]       |                           ^
[build] /space/pvelesko/chipStar/hip-tests-update/include/hip/devicelib/sync_and_util.hh:135:1: note: candidate function
[build]   135 | DECL_SHFL_OPS(double);
[build]       | ^
[build] /space/pvelesko/chipStar/hip-tests-update/include/hip/devicelib/sync_and_util.hh:121:27: note: expanded from macro 'DECL_SHFL_OPS'
[build]   121 |   extern __device__ TYPE_ __shfl(TYPE_ var, int srcLane,                       \
[build]       |                           ^
[build] /space/pvelesko/chipStar/hip-tests-update/include/hip/devicelib/sync_and_util.hh:149:20: note: candidate function
[build]   149 | DECL_LONGLONG_SHFL(__shfl, int);
[build]       |                    ^
[build] /space/pvelesko/chipStar/hip-tests-update/include/hip/devicelib/sync_and_util.hh:149:20: note: candidate function
[build] 1 error generated when compiling for .
[build] 
[build] failed to execute:/space/pvelesko/install/llvm/17.0/bin/clang++ -include /space/pvelesko/chipStar/hip-tests-update/include/hip/spirv_fixups.h -I//space/pvelesko/chipStar/hip-tests-update/build/include -I/space/pvelesko/chipStar/hip-tests-update/CHIP -I/space/pvelesko/chipStar/hip-tests-update/PUBLIC -I/usr/include/level_zero -I/space/pvelesko/chipStar/hip-tests-update/hip-tests/catch/external/Catch2 -I/space/pvelesko/chipStar/hip-tests-update/hip-tests/catch/./include -I/space/pvelesko/chipStar/hip-tests-update/hip-tests/catch/./kernels -I/space/pvelesko/chipStar/hip-tests-update/build/include -I/space/pvelesko/chipStar/hip-tests-update/hip-tests/catch/external/picojson -I/space/pvelesko/chipStar/hip-tests-update/build/catch -Wno-duplicate-decl-specifier -Wno-tautological-constant-compare -Wno-c++20-extensions -Wno-unused-result -Wno-delete-abstract-non-virtual-dtor -Wno-deprecated-declarations -Wunused-command-line-argument --std=c++17 -g -fPIE -Wno-format-extra-args -mf16c -Wall -O1 -std=c++17 -MD -c -x hip /space/pvelesko/chipStar/hip-tests-update/hip-tests/catch/unit/kernel/hipShflTests.cc -D__HIP_PLATFORM_SPIRV__= --offload=spirv64 -nohipwrapperinc --hip-path=/space/pvelesko/chipStar/hip-tests-update/build --target=x86_64-unknown-linux-gnu   -I/space/pvelesko/chipStar/hip-tests-update/include -I/space/pvelesko/chipStar/hip-tests-update/HIP/include -I/space/pvelesko/chipStar/hip-tests-update/build/include -o catch/catch_tests/unit/kernel/CMakeFiles/KernelTest.dir/hipShflTests.cc.o -MT catch/catch_tests/unit/kernel/CMakeFiles/KernelTest.dir/hipShflTests.cc.o -MF catch/catch_tests/unit/kernel/CMakeFiles/KernelTest.dir/hipShflTests.cc.o.d