xuhuisheng
commented
3 years ago CXX said it cannot find hsa_signal_wait_scacquire, the declaration of hsa_signal_wait_scacquire is in the /opt/rocm/include/hsa/hsa.h provided by ROCR-Runtime. Please check if there is old version - e.g. ROCm-4.1 installed on system.
UPDATE:
checked ROCm-4.1, also had this function https://github.com/RadeonOpenCompute/ROCR-Runtime/blob/rocm-4.1.x/src/inc/hsa.h#L1994 .
Please check the /opt/rocm/include/hsa/hsa.h to find out if there is hsa_signal_wait_scacquire or not. I suspect that this is other version of hsa.h.
I will try to put ROCm directory into rocm-build to try to reproduce this issue.
UPDATE: cannot reproduce on my environment. I created a clean ubuntu:20.04 docker and test.
~/rocm-build/build/rocclr ~/rocm-build/build/rocclr
-- The C compiler identification is GNU 9.3.0
-- The CXX compiler identification is GNU 9.3.0
-- Check for working C compiler: /usr/bin/cc
-- Check for working C compiler: /usr/bin/cc -- works
-- Detecting C compiler ABI info
-- Detecting C compiler ABI info - done
-- Detecting C compile features
-- Detecting C compile features - done
-- Check for working CXX compiler: /usr/bin/c++
-- Check for working CXX compiler: /usr/bin/c++ -- works
-- Detecting CXX compiler ABI info
-- Detecting CXX compiler ABI info - done
-- Detecting CXX compile features
-- Detecting CXX compile features - done
-- Code Object Manager found at /opt/rocm/lib/cmake/amd_comgr.
-- HSA Runtime found at /opt/rocm/lib/cmake/hsa-runtime64.
-- Looking for pthread.h
-- Looking for pthread.h - found
-- Performing Test CMAKE_HAVE_LIBC_PTHREAD
-- Performing Test CMAKE_HAVE_LIBC_PTHREAD - Failed
-- Check if compiler accepts -pthread
-- Check if compiler accepts -pthread - yes
-- Found Threads: TRUE
-- Found: /usr/lib/x86_64-linux-gnu/libnuma.so
-- Configuring done
-- Generating done
CMake Warning:
Manually-specified variables were not used by the project:
CPACK_GENERATOR
CPACK_PACKAGING_INSTALL_PREFIX
-- Build files have been written to: /home/work/rocm-build/build/rocclr
[39/47] Building CXX object CMakeFiles/amdrocclr_static.dir/device/device.cpp.o
/home/work/rocm-build/ROCm/ROCclr/device/device.cpp: In constructor 'amd::Device::Device()':
/home/work/rocm-build/ROCm/ROCclr/device/device.cpp:445:37: warning: 'void* memset(void*, int, size_t)' clearing an object of type 'struct device::Info' with no trivial copy-assignment; use assignment or value-initialization instead [-Wclass-memaccess]
445 | memset(&info_, '\0', sizeof(info_));
| ^
In file included from /home/work/rocm-build/ROCm/ROCclr/device/device.cpp:21:
/home/work/rocm-build/ROCm/ROCclr/device/device.hpp:222:8: note: 'struct device::Info' declared here
222 | struct Info : public amd::EmbeddedObject {
| ^~~~
[47/47] Linking CXX static library libamdrocclr_static.a
try again.
work@b8997d182ce7:~/rocm-build$ bash 18.rocclr.sh
Reading package lists... Done
Building dependency tree
Reading state information... Done
mesa-common-dev is already the newest version (20.2.6-0ubuntu0.20.04.1).
0 upgraded, 0 newly installed, 0 to remove and 5 not upgraded.
~/rocm-build/build/rocclr ~/rocm-build/build/rocclr
-- Code Object Manager found at /opt/rocm/lib/cmake/amd_comgr.
-- HSA Runtime found at /opt/rocm/lib/cmake/hsa-runtime64.
-- Found: /usr/lib/x86_64-linux-gnu/libnuma.so
-- Configuring done
-- Generating done
-- Build files have been written to: /home/work/rocm-build/build/rocclr
ninja: no work to do.
ianferreira
Environment
What is the expected behavior
Successfully build
Scripts 11-17 work well, breaks on 18.
What actually happens
bash 18.rocclr.sh
ian@ian-TRX40-AORUS-PRO-WIFI:~/Documents/rocm-build$ bash 18.rocclr.sh Reading package lists... Done Building dependency tree Reading state information... Done mesa-common-dev is already the newest version (20.2.6-0ubuntu0.20.04.1). The following packages were automatically installed and are no longer required: libllvm11.0-amdgpu llvm-amdgpu-11.0 llvm-amdgpu-11.0-dev llvm-amdgpu-11.0-runtime llvm-amdgpu-runtime Use 'sudo apt autoremove' to remove them. 0 upgraded, 0 newly installed, 0 to remove and 10 not upgraded. ~/Documents/rocm-build/build/rocclr ~/Documents/rocm-build/build/rocclr -- Code Object Manager found at /opt/rocm/lib/cmake/amd_comgr. -- HSA Runtime found at /opt/rocm/lib/cmake/hsa-runtime64. -- Found: /usr/lib/x86_64-linux-gnu/libnuma.so -- Configuring done -- Generating done -- Build files have been written to: /home/ian/Documents/rocm-build/build/rocclr [1/11] Building CXX object device/rocm/CMakeFiles/oclrocm.dir/rocsignal.cpp.o FAILED: device/rocm/CMakeFiles/oclrocm.dir/rocsignal.cpp.o /usr/bin/c++ -DATI_ARCH_X86 -DATI_BITS_64 -DATI_OS_LINUX -DCL_TARGET_OPENCL_VERSION=220 -DCL_USE_DEPRECATED_OPENCL_1_0_APIS -DCL_USE_DEPRECATED_OPENCL_1_1_APIS -DCL_USE_DEPRECATED_OPENCL_1_2_APIS -DCL_USE_DEPRECATED_OPENCL_2_0_APIS -DCOMGR_DYN_DLL -DLITTLEENDIAN_CPU -DOPENCL_C_MAJOR=2 -DOPENCL_C_MINOR=0 -DOPENCL_EXPORTS -DOPENCL_MAJOR=2 -DOPENCL_MINOR=1 -DROCCLR_SUPPORT_NUMA_POLICY -DUSE_COMGR_LIBRARY -DVEGA10_ONLY=false -DWITH_LIGHTNING_COMPILER -DWITH_TARGET_AMDGCN -D__x86_64__ -I/home/ian/Documents/rocm-build/ROCm/ROCclr -I/home/ian/Documents/rocm-build/ROCm/ROCclr/include -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime/khronos/headers -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime/khronos/headers/opencl2.2 -I/opt/rocm/include -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib/include -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib/backends/common -I/home/ian/Documents/rocm-build/ROCm/ROCclr/elf -Idevice/rocm -I/opt/rocm/include/hsa -fPIC -Wall -Wno-strict-aliasing -Wno-unused-variable -std=c++11 -MD -MT device/rocm/CMakeFiles/oclrocm.dir/rocsignal.cpp.o -MF device/rocm/CMakeFiles/oclrocm.dir/rocsignal.cpp.o.d -o device/rocm/CMakeFiles/oclrocm.dir/rocsignal.cpp.o -c /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocsignal.cpp /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocsignal.cpp: In member function ‘virtual uint64_t roc::Signal::Wait(uint64_t, device::Signal::Condition, uint64_t)’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocsignal.cpp:41:10: error: ‘hsa_signal_wait_scacquire’ was not declared in this scope; did you mean ‘hsa_signal_wait_acquire’? 41 | return hsa_signal_wait_scacquire( | ^~~~~~~~~~~~~~~~~~~~~~~~~ | hsa_signal_wait_acquire /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocsignal.cpp: In member function ‘virtual void roc::Signal::Reset(uint64_t)’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocsignal.cpp:50:3: error: ‘hsa_signal_store_screlease’ was not declared in this scope; did you mean ‘hsa_signal_store_release’? 50 | hsa_signal_store_screlease(signal_, value); | ^~~~~~~~~~~~~~~~~~~~~~~~~~ | hsa_signal_store_release [2/11] Building CXX object device/rocm/CMakeFiles/oclrocm.dir/rocmemory.cpp.o FAILED: device/rocm/CMakeFiles/oclrocm.dir/rocmemory.cpp.o /usr/bin/c++ -DATI_ARCH_X86 -DATI_BITS_64 -DATI_OS_LINUX -DCL_TARGET_OPENCL_VERSION=220 -DCL_USE_DEPRECATED_OPENCL_1_0_APIS -DCL_USE_DEPRECATED_OPENCL_1_1_APIS -DCL_USE_DEPRECATED_OPENCL_1_2_APIS -DCL_USE_DEPRECATED_OPENCL_2_0_APIS -DCOMGR_DYN_DLL -DLITTLEENDIAN_CPU -DOPENCL_C_MAJOR=2 -DOPENCL_C_MINOR=0 -DOPENCL_EXPORTS -DOPENCL_MAJOR=2 -DOPENCL_MINOR=1 -DROCCLR_SUPPORT_NUMA_POLICY -DUSE_COMGR_LIBRARY -DVEGA10_ONLY=false -DWITH_LIGHTNING_COMPILER -DWITH_TARGET_AMDGCN -D__x86_64__ -I/home/ian/Documents/rocm-build/ROCm/ROCclr -I/home/ian/Documents/rocm-build/ROCm/ROCclr/include -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime/khronos/headers -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime/khronos/headers/opencl2.2 -I/opt/rocm/include -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib/include -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib/backends/common -I/home/ian/Documents/rocm-build/ROCm/ROCclr/elf -Idevice/rocm -I/opt/rocm/include/hsa -fPIC -Wall -Wno-strict-aliasing -Wno-unused-variable -std=c++11 -MD -MT device/rocm/CMakeFiles/oclrocm.dir/rocmemory.cpp.o -MF device/rocm/CMakeFiles/oclrocm.dir/rocmemory.cpp.o.d -o device/rocm/CMakeFiles/oclrocm.dir/rocmemory.cpp.o -c /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocmemory.cpp In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.hpp:38, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocmemory.hpp:28, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocmemory.cpp:31: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp: In function ‘bool roc::WaitForSignal(hsa_signal_t)’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:62:9: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 62 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:62:9: note: (if you use ‘-fpermissive’, G++ will accept your code, but allowing the use of an undeclared name is deprecated) /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:70:9: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 70 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:73:11: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 73 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.hpp:46, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocmemory.hpp:28, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocmemory.cpp:31: /opt/rocm/include/hsa/hsa_ven_amd_loader.h: At global scope: /opt/rocm/include/hsa/hsa_ven_amd_loader.h:277:5: error: ‘hsa_loaded_code_object_t’ has not been declared 277 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:442:3: error: ‘hsa_loaded_code_object_t’ was not declared in this scope; did you mean ‘hsa_code_object_t’? 442 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:443:48: error: expected primary-expression before ‘attribute’ 443 | hsa_ven_amd_loader_loaded_code_object_info_t attribute, | ^~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:444:3: error: expected primary-expression before ‘void’ 444 | void *value); | ^~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:444:14: error: expression list treated as compound expression in initializer [-fpermissive] 444 | void *value); | ^ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:489:5: error: ‘hsa_file_t’ was not declared in this scope; did you mean ‘hsa_isa_t’? 489 | hsa_file_t file, | ^~~~~~~~~~ | hsa_isa_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:490:12: error: expected primary-expression before ‘offset’ 490 | size_t offset, | ^~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:491:12: error: expected primary-expression before ‘size’ 491 | size_t size, | ^~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:5: error: ‘hsa_code_object_reader_t’ was not declared in this scope; did you mean ‘hsa_code_object_type_t’? 492 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_type_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:31: error: ‘code_object_reader’ was not declared in this scope 492 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:49: error: expression list treated as compound expression in initializer [-fpermissive] 492 | hsa_code_object_reader_t *code_object_reader); | ^ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:538:7: error: ‘hsa_loaded_code_object_t’ has not been declared 538 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:543:5: error: ‘hsa_loaded_code_object_t’ has not been declared 543 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:568:7: error: ‘hsa_loaded_code_object_t’ has not been declared 568 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:573:5: error: ‘hsa_loaded_code_object_t’ has not been declared 573 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:579:7: error: ‘hsa_file_t’ has not been declared 579 | hsa_file_t file, | ^~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:582:7: error: ‘hsa_code_object_reader_t’ has not been declared 582 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~~~~~~~ [3/11] Building CXX object device/rocm/CMakeFiles/oclrocm.dir/rocprintf.cpp.o FAILED: device/rocm/CMakeFiles/oclrocm.dir/rocprintf.cpp.o /usr/bin/c++ -DATI_ARCH_X86 -DATI_BITS_64 -DATI_OS_LINUX -DCL_TARGET_OPENCL_VERSION=220 -DCL_USE_DEPRECATED_OPENCL_1_0_APIS -DCL_USE_DEPRECATED_OPENCL_1_1_APIS -DCL_USE_DEPRECATED_OPENCL_1_2_APIS -DCL_USE_DEPRECATED_OPENCL_2_0_APIS -DCOMGR_DYN_DLL -DLITTLEENDIAN_CPU -DOPENCL_C_MAJOR=2 -DOPENCL_C_MINOR=0 -DOPENCL_EXPORTS -DOPENCL_MAJOR=2 -DOPENCL_MINOR=1 -DROCCLR_SUPPORT_NUMA_POLICY -DUSE_COMGR_LIBRARY -DVEGA10_ONLY=false -DWITH_LIGHTNING_COMPILER -DWITH_TARGET_AMDGCN -D__x86_64__ -I/home/ian/Documents/rocm-build/ROCm/ROCclr -I/home/ian/Documents/rocm-build/ROCm/ROCclr/include -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime/khronos/headers -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime/khronos/headers/opencl2.2 -I/opt/rocm/include -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib/include -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib/backends/common -I/home/ian/Documents/rocm-build/ROCm/ROCclr/elf -Idevice/rocm -I/opt/rocm/include/hsa -fPIC -Wall -Wno-strict-aliasing -Wno-unused-variable -std=c++11 -MD -MT device/rocm/CMakeFiles/oclrocm.dir/rocprintf.cpp.o -MF device/rocm/CMakeFiles/oclrocm.dir/rocprintf.cpp.o.d -o device/rocm/CMakeFiles/oclrocm.dir/rocprintf.cpp.o -c /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprintf.cpp In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.hpp:38, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocmemory.hpp:28, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprintf.cpp:25: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp: In function ‘bool roc::WaitForSignal(hsa_signal_t)’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:62:9: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 62 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:62:9: note: (if you use ‘-fpermissive’, G++ will accept your code, but allowing the use of an undeclared name is deprecated) /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:70:9: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 70 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:73:11: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 73 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.hpp:46, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocmemory.hpp:28, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprintf.cpp:25: /opt/rocm/include/hsa/hsa_ven_amd_loader.h: At global scope: /opt/rocm/include/hsa/hsa_ven_amd_loader.h:277:5: error: ‘hsa_loaded_code_object_t’ has not been declared 277 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:442:3: error: ‘hsa_loaded_code_object_t’ was not declared in this scope; did you mean ‘hsa_code_object_t’? 442 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:443:48: error: expected primary-expression before ‘attribute’ 443 | hsa_ven_amd_loader_loaded_code_object_info_t attribute, | ^~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:444:3: error: expected primary-expression before ‘void’ 444 | void *value); | ^~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:444:14: error: expression list treated as compound expression in initializer [-fpermissive] 444 | void *value); | ^ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:489:5: error: ‘hsa_file_t’ was not declared in this scope; did you mean ‘hsa_isa_t’? 489 | hsa_file_t file, | ^~~~~~~~~~ | hsa_isa_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:490:12: error: expected primary-expression before ‘offset’ 490 | size_t offset, | ^~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:491:12: error: expected primary-expression before ‘size’ 491 | size_t size, | ^~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:5: error: ‘hsa_code_object_reader_t’ was not declared in this scope; did you mean ‘hsa_code_object_type_t’? 492 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_type_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:31: error: ‘code_object_reader’ was not declared in this scope 492 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:49: error: expression list treated as compound expression in initializer [-fpermissive] 492 | hsa_code_object_reader_t *code_object_reader); | ^ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:538:7: error: ‘hsa_loaded_code_object_t’ has not been declared 538 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:543:5: error: ‘hsa_loaded_code_object_t’ has not been declared 543 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:568:7: error: ‘hsa_loaded_code_object_t’ has not been declared 568 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:573:5: error: ‘hsa_loaded_code_object_t’ has not been declared 573 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:579:7: error: ‘hsa_file_t’ has not been declared 579 | hsa_file_t file, | ^~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:582:7: error: ‘hsa_code_object_reader_t’ has not been declared 582 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~~~~~~~ In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rockernel.hpp:25, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprintf.cpp:26: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.hpp:89:3: error: ‘hsa_code_object_reader_t’ does not name a type; did you mean ‘hsa_code_object_type_t’? 89 | hsa_code_object_reader_t hsaCodeObjectReader_; //!< Handle to HSA code reader | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_type_t [4/11] Building CXX object device/rocm/CMakeFiles/oclrocm.dir/rockernel.cpp.o FAILED: device/rocm/CMakeFiles/oclrocm.dir/rockernel.cpp.o /usr/bin/c++ -DATI_ARCH_X86 -DATI_BITS_64 -DATI_OS_LINUX -DCL_TARGET_OPENCL_VERSION=220 -DCL_USE_DEPRECATED_OPENCL_1_0_APIS -DCL_USE_DEPRECATED_OPENCL_1_1_APIS -DCL_USE_DEPRECATED_OPENCL_1_2_APIS -DCL_USE_DEPRECATED_OPENCL_2_0_APIS -DCOMGR_DYN_DLL -DLITTLEENDIAN_CPU -DOPENCL_C_MAJOR=2 -DOPENCL_C_MINOR=0 -DOPENCL_EXPORTS -DOPENCL_MAJOR=2 -DOPENCL_MINOR=1 -DROCCLR_SUPPORT_NUMA_POLICY -DUSE_COMGR_LIBRARY -DVEGA10_ONLY=false -DWITH_LIGHTNING_COMPILER -DWITH_TARGET_AMDGCN -D__x86_64__ -I/home/ian/Documents/rocm-build/ROCm/ROCclr -I/home/ian/Documents/rocm-build/ROCm/ROCclr/include -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime/khronos/headers -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime/khronos/headers/opencl2.2 -I/opt/rocm/include -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib/include -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib/backends/common -I/home/ian/Documents/rocm-build/ROCm/ROCclr/elf -Idevice/rocm -I/opt/rocm/include/hsa -fPIC -Wall -Wno-strict-aliasing -Wno-unused-variable -std=c++11 -MD -MT device/rocm/CMakeFiles/oclrocm.dir/rockernel.cpp.o -MF device/rocm/CMakeFiles/oclrocm.dir/rockernel.cpp.o.d -o device/rocm/CMakeFiles/oclrocm.dir/rockernel.cpp.o -c /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rockernel.cpp In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.hpp:38, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.hpp:30, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rockernel.hpp:25, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rockernel.cpp:21: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp: In function ‘bool roc::WaitForSignal(hsa_signal_t)’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:62:9: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 62 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:62:9: note: (if you use ‘-fpermissive’, G++ will accept your code, but allowing the use of an undeclared name is deprecated) /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:70:9: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 70 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:73:11: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 73 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.hpp:46, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.hpp:30, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rockernel.hpp:25, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rockernel.cpp:21: /opt/rocm/include/hsa/hsa_ven_amd_loader.h: At global scope: /opt/rocm/include/hsa/hsa_ven_amd_loader.h:277:5: error: ‘hsa_loaded_code_object_t’ has not been declared 277 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:442:3: error: ‘hsa_loaded_code_object_t’ was not declared in this scope; did you mean ‘hsa_code_object_t’? 442 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:443:48: error: expected primary-expression before ‘attribute’ 443 | hsa_ven_amd_loader_loaded_code_object_info_t attribute, | ^~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:444:3: error: expected primary-expression before ‘void’ 444 | void *value); | ^~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:444:14: error: expression list treated as compound expression in initializer [-fpermissive] 444 | void *value); | ^ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:489:5: error: ‘hsa_file_t’ was not declared in this scope; did you mean ‘hsa_isa_t’? 489 | hsa_file_t file, | ^~~~~~~~~~ | hsa_isa_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:490:12: error: expected primary-expression before ‘offset’ 490 | size_t offset, | ^~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:491:12: error: expected primary-expression before ‘size’ 491 | size_t size, | ^~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:5: error: ‘hsa_code_object_reader_t’ was not declared in this scope; did you mean ‘hsa_code_object_type_t’? 492 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_type_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:31: error: ‘code_object_reader’ was not declared in this scope 492 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:49: error: expression list treated as compound expression in initializer [-fpermissive] 492 | hsa_code_object_reader_t *code_object_reader); | ^ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:538:7: error: ‘hsa_loaded_code_object_t’ has not been declared 538 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:543:5: error: ‘hsa_loaded_code_object_t’ has not been declared 543 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:568:7: error: ‘hsa_loaded_code_object_t’ has not been declared 568 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:573:5: error: ‘hsa_loaded_code_object_t’ has not been declared 573 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:579:7: error: ‘hsa_file_t’ has not been declared 579 | hsa_file_t file, | ^~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:582:7: error: ‘hsa_code_object_reader_t’ has not been declared 582 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~~~~~~~ In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rockernel.hpp:25, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rockernel.cpp:21: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.hpp:89:3: error: ‘hsa_code_object_reader_t’ does not name a type; did you mean ‘hsa_code_object_type_t’? 89 | hsa_code_object_reader_t hsaCodeObjectReader_; //!< Handle to HSA code reader | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_type_t /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rockernel.cpp: In member function ‘virtual bool roc::LightningKernel::init()’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rockernel.cpp:75:15: error: ‘hsa_executable_get_symbol_by_name’ was not declared in this scope; did you mean ‘hsa_executable_get_symbol’? 75 | hsaStatus = hsa_executable_get_symbol_by_name(program()->hsaExecutable(), | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ | hsa_executable_get_symbol [5/11] Building CXX object device/rocm/CMakeFiles/oclrocm.dir/rocblit.cpp.o FAILED: device/rocm/CMakeFiles/oclrocm.dir/rocblit.cpp.o /usr/bin/c++ -DATI_ARCH_X86 -DATI_BITS_64 -DATI_OS_LINUX -DCL_TARGET_OPENCL_VERSION=220 -DCL_USE_DEPRECATED_OPENCL_1_0_APIS -DCL_USE_DEPRECATED_OPENCL_1_1_APIS -DCL_USE_DEPRECATED_OPENCL_1_2_APIS -DCL_USE_DEPRECATED_OPENCL_2_0_APIS -DCOMGR_DYN_DLL -DLITTLEENDIAN_CPU -DOPENCL_C_MAJOR=2 -DOPENCL_C_MINOR=0 -DOPENCL_EXPORTS -DOPENCL_MAJOR=2 -DOPENCL_MINOR=1 -DROCCLR_SUPPORT_NUMA_POLICY -DUSE_COMGR_LIBRARY -DVEGA10_ONLY=false -DWITH_LIGHTNING_COMPILER -DWITH_TARGET_AMDGCN -D__x86_64__ -I/home/ian/Documents/rocm-build/ROCm/ROCclr -I/home/ian/Documents/rocm-build/ROCm/ROCclr/include -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime/khronos/headers -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime/khronos/headers/opencl2.2 -I/opt/rocm/include -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib/include -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib/backends/common -I/home/ian/Documents/rocm-build/ROCm/ROCclr/elf -Idevice/rocm -I/opt/rocm/include/hsa -fPIC -Wall -Wno-strict-aliasing -Wno-unused-variable -std=c++11 -MD -MT device/rocm/CMakeFiles/oclrocm.dir/rocblit.cpp.o -MF device/rocm/CMakeFiles/oclrocm.dir/rocblit.cpp.o.d -o device/rocm/CMakeFiles/oclrocm.dir/rocblit.cpp.o -c /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocblit.cpp In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.hpp:38, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocblit.cpp:22: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp: In function ‘bool roc::WaitForSignal(hsa_signal_t)’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:62:9: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 62 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:62:9: note: (if you use ‘-fpermissive’, G++ will accept your code, but allowing the use of an undeclared name is deprecated) /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:70:9: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 70 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:73:11: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 73 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.hpp:46, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocblit.cpp:22: /opt/rocm/include/hsa/hsa_ven_amd_loader.h: At global scope: /opt/rocm/include/hsa/hsa_ven_amd_loader.h:277:5: error: ‘hsa_loaded_code_object_t’ has not been declared 277 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:442:3: error: ‘hsa_loaded_code_object_t’ was not declared in this scope; did you mean ‘hsa_code_object_t’? 442 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:443:48: error: expected primary-expression before ‘attribute’ 443 | hsa_ven_amd_loader_loaded_code_object_info_t attribute, | ^~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:444:3: error: expected primary-expression before ‘void’ 444 | void *value); | ^~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:444:14: error: expression list treated as compound expression in initializer [-fpermissive] 444 | void *value); | ^ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:489:5: error: ‘hsa_file_t’ was not declared in this scope; did you mean ‘hsa_isa_t’? 489 | hsa_file_t file, | ^~~~~~~~~~ | hsa_isa_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:490:12: error: expected primary-expression before ‘offset’ 490 | size_t offset, | ^~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:491:12: error: expected primary-expression before ‘size’ 491 | size_t size, | ^~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:5: error: ‘hsa_code_object_reader_t’ was not declared in this scope; did you mean ‘hsa_code_object_type_t’? 492 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_type_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:31: error: ‘code_object_reader’ was not declared in this scope 492 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:49: error: expression list treated as compound expression in initializer [-fpermissive] 492 | hsa_code_object_reader_t *code_object_reader); | ^ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:538:7: error: ‘hsa_loaded_code_object_t’ has not been declared 538 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:543:5: error: ‘hsa_loaded_code_object_t’ has not been declared 543 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:568:7: error: ‘hsa_loaded_code_object_t’ has not been declared 568 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:573:5: error: ‘hsa_loaded_code_object_t’ has not been declared 573 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:579:7: error: ‘hsa_file_t’ has not been declared 579 | hsa_file_t file, | ^~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:582:7: error: ‘hsa_code_object_reader_t’ has not been declared 582 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~~~~~~~ In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rockernel.hpp:25, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocblit.cpp:25: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.hpp:89:3: error: ‘hsa_code_object_reader_t’ does not name a type; did you mean ‘hsa_code_object_type_t’? 89 | hsa_code_object_reader_t hsaCodeObjectReader_; //!< Handle to HSA code reader | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_type_t In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.hpp:38, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocblit.cpp:22: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp: In instantiation of ‘bool roc::WaitForSignal(hsa_signal_t) [with long unsigned int wait_time = 0; hsa_signal_t = hsa_signal_s]’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocblit.cpp:2435:37: required from here /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:62:34: error: ‘hsa_signal_wait_scacquire’ was not declared in this scope; did you mean ‘hsa_signal_wait_acquire’? 62 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ 63 | wait_time, HSA_WAIT_STATE_ACTIVE) != 0) { | ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:70:34: error: ‘hsa_signal_wait_scacquire’ was not declared in this scope; did you mean ‘hsa_signal_wait_acquire’? 70 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ 71 | timeout, HSA_WAIT_STATE_ACTIVE) != 0) { | ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:73:36: error: ‘hsa_signal_wait_scacquire’ was not declared in this scope, and no declarations were found by argument-dependent lookup at the point of instantiation [-fpermissive] 73 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ 74 | kUnlimitedWait, HSA_WAIT_STATE_BLOCKED) != 0) { | ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ [6/11] Building CXX object CMakeFiles/amdrocclr_static.dir/device/device.cpp.o FAILED: CMakeFiles/amdrocclr_static.dir/device/device.cpp.o /usr/bin/c++ -DATI_ARCH_X86 -DATI_BITS_64 -DATI_OS_LINUX -DCL_TARGET_OPENCL_VERSION=220 -DCL_USE_DEPRECATED_OPENCL_1_0_APIS -DCL_USE_DEPRECATED_OPENCL_1_1_APIS -DCL_USE_DEPRECATED_OPENCL_1_2_APIS -DCL_USE_DEPRECATED_OPENCL_2_0_APIS -DCOMGR_DYN_DLL -DLITTLEENDIAN_CPU -DOPENCL_C_MAJOR=2 -DOPENCL_C_MINOR=0 -DOPENCL_EXPORTS -DOPENCL_MAJOR=2 -DOPENCL_MINOR=1 -DUSE_COMGR_LIBRARY -DVEGA10_ONLY=false -DWITH_HSA_DEVICE -DWITH_LIGHTNING_COMPILER -DWITH_TARGET_AMDGCN -D__x86_64__ -I/home/ian/Documents/rocm-build/ROCm/ROCclr -I/home/ian/Documents/rocm-build/ROCm/ROCclr/include -I/home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib/include -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib/backends/common -I/home/ian/Documents/rocm-build/ROCm/ROCclr/elf -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime/khronos/headers -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime/khronos/headers/opencl2.2 -isystem /opt/rocm/include -isystem /opt/rocm/include/hsa -fPIC -Wall -Wno-strict-aliasing -Wno-unused-variable -pthread -std=c++11 -MD -MT CMakeFiles/amdrocclr_static.dir/device/device.cpp.o -MF CMakeFiles/amdrocclr_static.dir/device/device.cpp.o.d -o CMakeFiles/amdrocclr_static.dir/device/device.cpp.o -c /home/ian/Documents/rocm-build/ROCm/ROCclr/device/device.cpp In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.hpp:38, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/device.cpp:32: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp: In function ‘bool roc::WaitForSignal(hsa_signal_t)’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:62:9: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 62 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:62:9: note: (if you use ‘-fpermissive’, G++ will accept your code, but allowing the use of an undeclared name is deprecated) /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:70:9: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 70 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:73:11: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 73 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.hpp:46, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/device.cpp:32: /opt/rocm/include/hsa/hsa_ven_amd_loader.h: At global scope: /opt/rocm/include/hsa/hsa_ven_amd_loader.h:277:5: error: ‘hsa_loaded_code_object_t’ has not been declared 277 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:442:3: error: ‘hsa_loaded_code_object_t’ was not declared in this scope; did you mean ‘hsa_code_object_t’? 442 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:443:48: error: expected primary-expression before ‘attribute’ 443 | hsa_ven_amd_loader_loaded_code_object_info_t attribute, | ^~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:444:3: error: expected primary-expression before ‘void’ 444 | void *value); | ^~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:444:14: error: expression list treated as compound expression in initializer [-fpermissive] 444 | void *value); | ^ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:489:5: error: ‘hsa_file_t’ was not declared in this scope; did you mean ‘hsa_isa_t’? 489 | hsa_file_t file, | ^~~~~~~~~~ | hsa_isa_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:490:12: error: expected primary-expression before ‘offset’ 490 | size_t offset, | ^~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:491:12: error: expected primary-expression before ‘size’ 491 | size_t size, | ^~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:5: error: ‘hsa_code_object_reader_t’ was not declared in this scope; did you mean ‘hsa_code_object_type_t’? 492 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_type_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:31: error: ‘code_object_reader’ was not declared in this scope 492 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:49: error: expression list treated as compound expression in initializer [-fpermissive] 492 | hsa_code_object_reader_t *code_object_reader); | ^ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:538:7: error: ‘hsa_loaded_code_object_t’ has not been declared 538 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:543:5: error: ‘hsa_loaded_code_object_t’ has not been declared 543 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:568:7: error: ‘hsa_loaded_code_object_t’ has not been declared 568 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:573:5: error: ‘hsa_loaded_code_object_t’ has not been declared 573 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:579:7: error: ‘hsa_file_t’ has not been declared 579 | hsa_file_t file, | ^~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:582:7: error: ‘hsa_code_object_reader_t’ has not been declared 582 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/device.cpp: In constructor ‘amd::Device::Device()’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/device.cpp:445:37: warning: ‘void* memset(void*, int, size_t)’ clearing an object of type ‘struct device::Info’ with no trivial copy-assignment; use assignment or value-initialization instead [-Wclass-memaccess] 445 | memset(&info_, '\0', sizeof(info_)); | ^ In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/device.cpp:21: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/device.hpp:222:8: note: ‘struct device::Info’ declared here 222 | struct Info : public amd::EmbeddedObject { | ^~~~ [7/11] Building CXX object device/rocm/CMakeFiles/oclrocm.dir/roccounters.cpp.o FAILED: device/rocm/CMakeFiles/oclrocm.dir/roccounters.cpp.o /usr/bin/c++ -DATI_ARCH_X86 -DATI_BITS_64 -DATI_OS_LINUX -DCL_TARGET_OPENCL_VERSION=220 -DCL_USE_DEPRECATED_OPENCL_1_0_APIS -DCL_USE_DEPRECATED_OPENCL_1_1_APIS -DCL_USE_DEPRECATED_OPENCL_1_2_APIS -DCL_USE_DEPRECATED_OPENCL_2_0_APIS -DCOMGR_DYN_DLL -DLITTLEENDIAN_CPU -DOPENCL_C_MAJOR=2 -DOPENCL_C_MINOR=0 -DOPENCL_EXPORTS -DOPENCL_MAJOR=2 -DOPENCL_MINOR=1 -DROCCLR_SUPPORT_NUMA_POLICY -DUSE_COMGR_LIBRARY -DVEGA10_ONLY=false -DWITH_LIGHTNING_COMPILER -DWITH_TARGET_AMDGCN -D__x86_64__ -I/home/ian/Documents/rocm-build/ROCm/ROCclr -I/home/ian/Documents/rocm-build/ROCm/ROCclr/include -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime/khronos/headers -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime/khronos/headers/opencl2.2 -I/opt/rocm/include -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib/include -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib/backends/common -I/home/ian/Documents/rocm-build/ROCm/ROCclr/elf -Idevice/rocm -I/opt/rocm/include/hsa -fPIC -Wall -Wno-strict-aliasing -Wno-unused-variable -std=c++11 -MD -MT device/rocm/CMakeFiles/oclrocm.dir/roccounters.cpp.o -MF device/rocm/CMakeFiles/oclrocm.dir/roccounters.cpp.o.d -o device/rocm/CMakeFiles/oclrocm.dir/roccounters.cpp.o -c /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/roccounters.cpp In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.hpp:38, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/roccounters.hpp:26, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/roccounters.cpp:21: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp: In function ‘bool roc::WaitForSignal(hsa_signal_t)’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:62:9: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 62 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:62:9: note: (if you use ‘-fpermissive’, G++ will accept your code, but allowing the use of an undeclared name is deprecated) /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:70:9: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 70 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:73:11: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 73 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.hpp:46, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/roccounters.hpp:26, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/roccounters.cpp:21: /opt/rocm/include/hsa/hsa_ven_amd_loader.h: At global scope: /opt/rocm/include/hsa/hsa_ven_amd_loader.h:277:5: error: ‘hsa_loaded_code_object_t’ has not been declared 277 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:442:3: error: ‘hsa_loaded_code_object_t’ was not declared in this scope; did you mean ‘hsa_code_object_t’? 442 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:443:48: error: expected primary-expression before ‘attribute’ 443 | hsa_ven_amd_loader_loaded_code_object_info_t attribute, | ^~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:444:3: error: expected primary-expression before ‘void’ 444 | void *value); | ^~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:444:14: error: expression list treated as compound expression in initializer [-fpermissive] 444 | void *value); | ^ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:489:5: error: ‘hsa_file_t’ was not declared in this scope; did you mean ‘hsa_isa_t’? 489 | hsa_file_t file, | ^~~~~~~~~~ | hsa_isa_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:490:12: error: expected primary-expression before ‘offset’ 490 | size_t offset, | ^~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:491:12: error: expected primary-expression before ‘size’ 491 | size_t size, | ^~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:5: error: ‘hsa_code_object_reader_t’ was not declared in this scope; did you mean ‘hsa_code_object_type_t’? 492 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_type_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:31: error: ‘code_object_reader’ was not declared in this scope 492 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:49: error: expression list treated as compound expression in initializer [-fpermissive] 492 | hsa_code_object_reader_t *code_object_reader); | ^ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:538:7: error: ‘hsa_loaded_code_object_t’ has not been declared 538 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:543:5: error: ‘hsa_loaded_code_object_t’ has not been declared 543 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:568:7: error: ‘hsa_loaded_code_object_t’ has not been declared 568 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:573:5: error: ‘hsa_loaded_code_object_t’ has not been declared 573 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:579:7: error: ‘hsa_file_t’ has not been declared 579 | hsa_file_t file, | ^~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:582:7: error: ‘hsa_code_object_reader_t’ has not been declared 582 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~~~~~~~ In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/roccounters.cpp:21: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/roccounters.hpp: In member function ‘bool roc::PerfCounterProfile::Create()’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/roccounters.hpp:121:36: error: ‘HSA_EXTENSION_AMD_AQLPROFILE’ was not declared in this scope; did you mean ‘HSA_EXTENSION_AMD_PROFILER’? 121 | hsa_system_extension_supported(HSA_EXTENSION_AMD_AQLPROFILE, 1, 0, &system_support); | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~ | HSA_EXTENSION_AMD_PROFILER /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/roccounters.hpp:127:9: error: ‘hsa_system_get_major_extension_table’ was not declared in this scope; did you mean ‘hsa_system_get_extension_table’? 127 | if (hsa_system_get_major_extension_table(HSA_EXTENSION_AMD_AQLPROFILE, | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ | hsa_system_get_extension_table [8/11] Building CXX object device/rocm/CMakeFiles/oclrocm.dir/rocprogram.cpp.o FAILED: device/rocm/CMakeFiles/oclrocm.dir/rocprogram.cpp.o /usr/bin/c++ -DATI_ARCH_X86 -DATI_BITS_64 -DATI_OS_LINUX -DCL_TARGET_OPENCL_VERSION=220 -DCL_USE_DEPRECATED_OPENCL_1_0_APIS -DCL_USE_DEPRECATED_OPENCL_1_1_APIS -DCL_USE_DEPRECATED_OPENCL_1_2_APIS -DCL_USE_DEPRECATED_OPENCL_2_0_APIS -DCOMGR_DYN_DLL -DLITTLEENDIAN_CPU -DOPENCL_C_MAJOR=2 -DOPENCL_C_MINOR=0 -DOPENCL_EXPORTS -DOPENCL_MAJOR=2 -DOPENCL_MINOR=1 -DROCCLR_SUPPORT_NUMA_POLICY -DUSE_COMGR_LIBRARY -DVEGA10_ONLY=false -DWITH_LIGHTNING_COMPILER -DWITH_TARGET_AMDGCN -D__x86_64__ -I/home/ian/Documents/rocm-build/ROCm/ROCclr -I/home/ian/Documents/rocm-build/ROCm/ROCclr/include -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime/khronos/headers -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime/khronos/headers/opencl2.2 -I/opt/rocm/include -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib/include -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib/backends/common -I/home/ian/Documents/rocm-build/ROCm/ROCclr/elf -Idevice/rocm -I/opt/rocm/include/hsa -fPIC -Wall -Wno-strict-aliasing -Wno-unused-variable -std=c++11 -MD -MT device/rocm/CMakeFiles/oclrocm.dir/rocprogram.cpp.o -MF device/rocm/CMakeFiles/oclrocm.dir/rocprogram.cpp.o.d -o device/rocm/CMakeFiles/oclrocm.dir/rocprogram.cpp.o -c /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.cpp In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.hpp:38, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.hpp:30, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.cpp:23: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp: In function ‘bool roc::WaitForSignal(hsa_signal_t)’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:62:9: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 62 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:62:9: note: (if you use ‘-fpermissive’, G++ will accept your code, but allowing the use of an undeclared name is deprecated) /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:70:9: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 70 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:73:11: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 73 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.hpp:46, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.hpp:30, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.cpp:23: /opt/rocm/include/hsa/hsa_ven_amd_loader.h: At global scope: /opt/rocm/include/hsa/hsa_ven_amd_loader.h:277:5: error: ‘hsa_loaded_code_object_t’ has not been declared 277 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:442:3: error: ‘hsa_loaded_code_object_t’ was not declared in this scope; did you mean ‘hsa_code_object_t’? 442 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:443:48: error: expected primary-expression before ‘attribute’ 443 | hsa_ven_amd_loader_loaded_code_object_info_t attribute, | ^~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:444:3: error: expected primary-expression before ‘void’ 444 | void *value); | ^~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:444:14: error: expression list treated as compound expression in initializer [-fpermissive] 444 | void *value); | ^ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:489:5: error: ‘hsa_file_t’ was not declared in this scope; did you mean ‘hsa_isa_t’? 489 | hsa_file_t file, | ^~~~~~~~~~ | hsa_isa_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:490:12: error: expected primary-expression before ‘offset’ 490 | size_t offset, | ^~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:491:12: error: expected primary-expression before ‘size’ 491 | size_t size, | ^~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:5: error: ‘hsa_code_object_reader_t’ was not declared in this scope; did you mean ‘hsa_code_object_type_t’? 492 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_type_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:31: error: ‘code_object_reader’ was not declared in this scope 492 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:49: error: expression list treated as compound expression in initializer [-fpermissive] 492 | hsa_code_object_reader_t *code_object_reader); | ^ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:538:7: error: ‘hsa_loaded_code_object_t’ has not been declared 538 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:543:5: error: ‘hsa_loaded_code_object_t’ has not been declared 543 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:568:7: error: ‘hsa_loaded_code_object_t’ has not been declared 568 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:573:5: error: ‘hsa_loaded_code_object_t’ has not been declared 573 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:579:7: error: ‘hsa_file_t’ has not been declared 579 | hsa_file_t file, | ^~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:582:7: error: ‘hsa_code_object_reader_t’ has not been declared 582 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~~~~~~~ In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.cpp:23: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.hpp:89:3: error: ‘hsa_code_object_reader_t’ does not name a type; did you mean ‘hsa_code_object_type_t’? 89 | hsa_code_object_reader_t hsaCodeObjectReader_; //!< Handle to HSA code reader | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_type_t /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.cpp: In destructor ‘virtual roc::Program::~Program()’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.cpp:78:7: error: ‘hsaCodeObjectReader_’ was not declared in this scope 78 | if (hsaCodeObjectReader_.handle != 0) { | ^~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.cpp:79:5: error: ‘hsa_code_object_reader_destroy’ was not declared in this scope; did you mean ‘hsa_code_object_destroy’? 79 | hsa_code_object_reader_destroy(hsaCodeObjectReader_); | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_destroy /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.cpp: In constructor ‘roc::Program::Program(roc::NullDevice&, amd::Program&)’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.cpp:86:3: error: ‘hsaCodeObjectReader_’ was not declared in this scope 86 | hsaCodeObjectReader_.handle = 0; | ^~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.cpp: In member function ‘virtual bool roc::Program::createGlobalVarObj(amd::Memory**, void**, size_t*, const char*) const’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.cpp:167:12: error: ‘hsa_executable_get_symbol_by_name’ was not declared in this scope; did you mean ‘hsa_executable_get_symbol’? 167 | status = hsa_executable_get_symbol_by_name(hsaExecutable_, global_name, &hsa_device, | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ | hsa_executable_get_symbol /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.cpp: In member function ‘virtual bool roc::LightningProgram::setKernels(amd::option::Options*, void*, size_t, amd::Os::FileDesc, size_t, std::string)’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.cpp:495:12: error: ‘hsa_executable_create_alt’ was not declared in this scope; did you mean ‘hsa_executable_create’? 495 | status = hsa_executable_create_alt(HSA_PROFILE_FULL, HSA_DEFAULT_FLOAT_ROUNDING_MODE_DEFAULT, | ^~~~~~~~~~~~~~~~~~~~~~~~~ | hsa_executable_create /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.cpp:507:72: error: ‘hsaCodeObjectReader_’ was not declared in this scope 507 | status = hsa_code_object_reader_create_from_memory(binary, binSize, &hsaCodeObjectReader_); | ^~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.cpp:507:12: error: ‘hsa_code_object_reader_create_from_memory’ was not declared in this scope 507 | status = hsa_code_object_reader_create_from_memory(binary, binSize, &hsaCodeObjectReader_); | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.cpp:515:12: error: ‘hsa_executable_load_agent_code_object’ was not declared in this scope; did you mean ‘hsa_executable_load_code_object’? 515 | status = hsa_executable_load_agent_code_object(hsaExecutable_, agent, hsaCodeObjectReader_, nullptr, | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ | hsa_executable_load_code_object [9/11] Building CXX object device/rocm/CMakeFiles/oclrocm.dir/rocdevice.cpp.o FAILED: device/rocm/CMakeFiles/oclrocm.dir/rocdevice.cpp.o /usr/bin/c++ -DATI_ARCH_X86 -DATI_BITS_64 -DATI_OS_LINUX -DCL_TARGET_OPENCL_VERSION=220 -DCL_USE_DEPRECATED_OPENCL_1_0_APIS -DCL_USE_DEPRECATED_OPENCL_1_1_APIS -DCL_USE_DEPRECATED_OPENCL_1_2_APIS -DCL_USE_DEPRECATED_OPENCL_2_0_APIS -DCOMGR_DYN_DLL -DLITTLEENDIAN_CPU -DOPENCL_C_MAJOR=2 -DOPENCL_C_MINOR=0 -DOPENCL_EXPORTS -DOPENCL_MAJOR=2 -DOPENCL_MINOR=1 -DROCCLR_SUPPORT_NUMA_POLICY -DUSE_COMGR_LIBRARY -DVEGA10_ONLY=false -DWITH_LIGHTNING_COMPILER -DWITH_TARGET_AMDGCN -D__x86_64__ -I/home/ian/Documents/rocm-build/ROCm/ROCclr -I/home/ian/Documents/rocm-build/ROCm/ROCclr/include -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime/khronos/headers -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime/khronos/headers/opencl2.2 -I/opt/rocm/include -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib/include -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib/backends/common -I/home/ian/Documents/rocm-build/ROCm/ROCclr/elf -Idevice/rocm -I/opt/rocm/include/hsa -fPIC -Wall -Wno-strict-aliasing -Wno-unused-variable -std=c++11 -MD -MT device/rocm/CMakeFiles/oclrocm.dir/rocdevice.cpp.o -MF device/rocm/CMakeFiles/oclrocm.dir/rocdevice.cpp.o.d -o device/rocm/CMakeFiles/oclrocm.dir/rocdevice.cpp.o -c /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.cpp In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.hpp:38, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.cpp:36: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp: In function ‘bool roc::WaitForSignal(hsa_signal_t)’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:62:9: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 62 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:62:9: note: (if you use ‘-fpermissive’, G++ will accept your code, but allowing the use of an undeclared name is deprecated) /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:70:9: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 70 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:73:11: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 73 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.hpp:46, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.cpp:36: /opt/rocm/include/hsa/hsa_ven_amd_loader.h: At global scope: /opt/rocm/include/hsa/hsa_ven_amd_loader.h:277:5: error: ‘hsa_loaded_code_object_t’ has not been declared 277 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:442:3: error: ‘hsa_loaded_code_object_t’ was not declared in this scope; did you mean ‘hsa_code_object_t’? 442 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:443:48: error: expected primary-expression before ‘attribute’ 443 | hsa_ven_amd_loader_loaded_code_object_info_t attribute, | ^~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:444:3: error: expected primary-expression before ‘void’ 444 | void *value); | ^~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:444:14: error: expression list treated as compound expression in initializer [-fpermissive] 444 | void *value); | ^ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:489:5: error: ‘hsa_file_t’ was not declared in this scope; did you mean ‘hsa_isa_t’? 489 | hsa_file_t file, | ^~~~~~~~~~ | hsa_isa_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:490:12: error: expected primary-expression before ‘offset’ 490 | size_t offset, | ^~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:491:12: error: expected primary-expression before ‘size’ 491 | size_t size, | ^~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:5: error: ‘hsa_code_object_reader_t’ was not declared in this scope; did you mean ‘hsa_code_object_type_t’? 492 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_type_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:31: error: ‘code_object_reader’ was not declared in this scope 492 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:49: error: expression list treated as compound expression in initializer [-fpermissive] 492 | hsa_code_object_reader_t *code_object_reader); | ^ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:538:7: error: ‘hsa_loaded_code_object_t’ has not been declared 538 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:543:5: error: ‘hsa_loaded_code_object_t’ has not been declared 543 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:568:7: error: ‘hsa_loaded_code_object_t’ has not been declared 568 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:573:5: error: ‘hsa_loaded_code_object_t’ has not been declared 573 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:579:7: error: ‘hsa_file_t’ has not been declared 579 | hsa_file_t file, | ^~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:582:7: error: ‘hsa_code_object_reader_t’ has not been declared 582 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~~~~~~~ In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.cpp:39: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.hpp:89:3: error: ‘hsa_code_object_reader_t’ does not name a type; did you mean ‘hsa_code_object_type_t’? 89 | hsa_code_object_reader_t hsaCodeObjectReader_; //!< Handle to HSA code reader | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_type_t /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.cpp: In static member function ‘static bool roc::Device::init()’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.cpp:469:40: error: ‘HSA_EXTENSION_AMD_LOADER’ was not declared in this scope; did you mean ‘HSA_EXTENSION_AMD_PROFILER’? 469 | hsa_system_get_major_extension_table(HSA_EXTENSION_AMD_LOADER, 1, sizeof(amd_loader_ext_table), | ^~~~~~~~~~~~~~~~~~~~~~~~ | HSA_EXTENSION_AMD_PROFILER /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.cpp:469:3: error: ‘hsa_system_get_major_extension_table’ was not declared in this scope; did you mean ‘hsa_system_get_extension_table’? 469 | hsa_system_get_major_extension_table(HSA_EXTENSION_AMD_LOADER, 1, sizeof(amd_loader_ext_table), | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ | hsa_system_get_extension_table /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.cpp: In member function ‘bool roc::Device::create()’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.cpp:590:7: error: ‘hsa_agent_iterate_isas’ was not declared in this scope; did you mean ‘hsa_agent_iterate_regions’? 590 | hsa_agent_iterate_isas(_bkendDevice, | ^~~~~~~~~~~~~~~~~~~~~~ | hsa_agent_iterate_regions /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.cpp:611:7: error: ‘hsa_isa_get_info_alt’ was not declared in this scope; did you mean ‘hsa_isa_get_info’? 611 | hsa_isa_get_info_alt(agent_isas.first_isa, (hsa_isa_info_t)HSA_ISA_INFO_NAME_LENGTH, | ^~~~~~~~~~~~~~~~~~~~ | hsa_isa_get_info /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.cpp:620:7: error: ‘hsa_isa_get_info_alt’ was not declared in this scope; did you mean ‘hsa_isa_get_info’? 620 | hsa_isa_get_info_alt(agent_isas.first_isa, (hsa_isa_info_t)HSA_ISA_INFO_NAME, | ^~~~~~~~~~~~~~~~~~~~ | hsa_isa_get_info /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.cpp: In member function ‘hsa_queue_t* roc::Device::acquireQueue(uint32_t, bool, const std::vector<unsigned int>&, amd::CommandQueue::Priority)’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.cpp:2609:18: error: ‘HSA_QUEUE_TYPE_COOPERATIVE’ was not declared in this scope; did you mean ‘HSA_QUEUE_TYPE_MULTI’? 2609 | queue_type = HSA_QUEUE_TYPE_COOPERATIVE; | ^~~~~~~~~~~~~~~~~~~~~~~~~~ | HSA_QUEUE_TYPE_MULTI [10/11] Building CXX object device/rocm/CMakeFiles/oclrocm.dir/rocvirtual.cpp.o FAILED: device/rocm/CMakeFiles/oclrocm.dir/rocvirtual.cpp.o /usr/bin/c++ -DATI_ARCH_X86 -DATI_BITS_64 -DATI_OS_LINUX -DCL_TARGET_OPENCL_VERSION=220 -DCL_USE_DEPRECATED_OPENCL_1_0_APIS -DCL_USE_DEPRECATED_OPENCL_1_1_APIS -DCL_USE_DEPRECATED_OPENCL_1_2_APIS -DCL_USE_DEPRECATED_OPENCL_2_0_APIS -DCOMGR_DYN_DLL -DLITTLEENDIAN_CPU -DOPENCL_C_MAJOR=2 -DOPENCL_C_MINOR=0 -DOPENCL_EXPORTS -DOPENCL_MAJOR=2 -DOPENCL_MINOR=1 -DROCCLR_SUPPORT_NUMA_POLICY -DUSE_COMGR_LIBRARY -DVEGA10_ONLY=false -DWITH_LIGHTNING_COMPILER -DWITH_TARGET_AMDGCN -D__x86_64__ -I/home/ian/Documents/rocm-build/ROCm/ROCclr -I/home/ian/Documents/rocm-build/ROCm/ROCclr/include -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime/khronos/headers -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime/khronos/headers/opencl2.2 -I/opt/rocm/include -I/home/ian/Documents/rocm-build/ROCm/ROCm-OpenCL-Runtime -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib/include -I/home/ian/Documents/rocm-build/ROCm/ROCclr/compiler/lib/backends/common -I/home/ian/Documents/rocm-build/ROCm/ROCclr/elf -Idevice/rocm -I/opt/rocm/include/hsa -fPIC -Wall -Wno-strict-aliasing -Wno-unused-variable -std=c++11 -MD -MT device/rocm/CMakeFiles/oclrocm.dir/rocvirtual.cpp.o -MF device/rocm/CMakeFiles/oclrocm.dir/rocvirtual.cpp.o.d -o device/rocm/CMakeFiles/oclrocm.dir/rocvirtual.cpp.o -c /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.hpp:38, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:22: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp: In function ‘bool roc::WaitForSignal(hsa_signal_t)’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:62:9: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 62 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:62:9: note: (if you use ‘-fpermissive’, G++ will accept your code, but allowing the use of an undeclared name is deprecated) /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:70:9: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 70 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:73:11: error: there are no arguments to ‘hsa_signal_wait_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_signal_wait_scacquire’ must be available [-fpermissive] 73 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ^~~~~~~~~~~~~~~~~~~~~~~~~ In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.hpp:46, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:22: /opt/rocm/include/hsa/hsa_ven_amd_loader.h: At global scope: /opt/rocm/include/hsa/hsa_ven_amd_loader.h:277:5: error: ‘hsa_loaded_code_object_t’ has not been declared 277 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:442:3: error: ‘hsa_loaded_code_object_t’ was not declared in this scope; did you mean ‘hsa_code_object_t’? 442 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:443:48: error: expected primary-expression before ‘attribute’ 443 | hsa_ven_amd_loader_loaded_code_object_info_t attribute, | ^~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:444:3: error: expected primary-expression before ‘void’ 444 | void *value); | ^~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:444:14: error: expression list treated as compound expression in initializer [-fpermissive] 444 | void *value); | ^ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:489:5: error: ‘hsa_file_t’ was not declared in this scope; did you mean ‘hsa_isa_t’? 489 | hsa_file_t file, | ^~~~~~~~~~ | hsa_isa_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:490:12: error: expected primary-expression before ‘offset’ 490 | size_t offset, | ^~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:491:12: error: expected primary-expression before ‘size’ 491 | size_t size, | ^~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:5: error: ‘hsa_code_object_reader_t’ was not declared in this scope; did you mean ‘hsa_code_object_type_t’? 492 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_type_t /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:31: error: ‘code_object_reader’ was not declared in this scope 492 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:492:49: error: expression list treated as compound expression in initializer [-fpermissive] 492 | hsa_code_object_reader_t *code_object_reader); | ^ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:538:7: error: ‘hsa_loaded_code_object_t’ has not been declared 538 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:543:5: error: ‘hsa_loaded_code_object_t’ has not been declared 543 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:568:7: error: ‘hsa_loaded_code_object_t’ has not been declared 568 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:573:5: error: ‘hsa_loaded_code_object_t’ has not been declared 573 | hsa_loaded_code_object_t loaded_code_object, | ^~~~~~~~~~~~~~~~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:579:7: error: ‘hsa_file_t’ has not been declared 579 | hsa_file_t file, | ^~~~~~~~~~ /opt/rocm/include/hsa/hsa_ven_amd_loader.h:582:7: error: ‘hsa_code_object_reader_t’ has not been declared 582 | hsa_code_object_reader_t *code_object_reader); | ^~~~~~~~~~~~~~~~~~~~~~~~ In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rockernel.hpp:25, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:24: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocprogram.hpp:89:3: error: ‘hsa_code_object_reader_t’ does not name a type; did you mean ‘hsa_code_object_type_t’? 89 | hsa_code_object_reader_t hsaCodeObjectReader_; //!< Handle to HSA code reader | ^~~~~~~~~~~~~~~~~~~~~~~~ | hsa_code_object_type_t In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:27: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/roccounters.hpp: In member function ‘bool roc::PerfCounterProfile::Create()’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/roccounters.hpp:121:36: error: ‘HSA_EXTENSION_AMD_AQLPROFILE’ was not declared in this scope; did you mean ‘HSA_EXTENSION_AMD_PROFILER’? 121 | hsa_system_extension_supported(HSA_EXTENSION_AMD_AQLPROFILE, 1, 0, &system_support); | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~ | HSA_EXTENSION_AMD_PROFILER /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/roccounters.hpp:127:9: error: ‘hsa_system_get_major_extension_table’ was not declared in this scope; did you mean ‘hsa_system_get_extension_table’? 127 | if (hsa_system_get_major_extension_table(HSA_EXTENSION_AMD_AQLPROFILE, | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ | hsa_system_get_extension_table /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp: In member function ‘hsa_signal_t roc::VirtualGPU::HwQueueTracker::ActiveSignal(hsa_signal_value_t, roc::Timestamp*, uint32_t)’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:328:3: error: ‘hsa_signal_silent_store_relaxed’ was not declared in this scope; did you mean ‘hsa_signal_store_relaxed’? 328 | hsa_signal_silent_store_relaxed(prof_signal->signal_, init_val); | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ | hsa_signal_store_relaxed /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp: In member function ‘void roc::VirtualGPU::HwQueueTracker::ResetCurrentSignal()’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:429:3: error: ‘hsa_signal_silent_store_relaxed’ was not declared in this scope; did you mean ‘hsa_signal_store_relaxed’? 429 | hsa_signal_silent_store_relaxed(signal_list_[current_id_]->signal_, 0); | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ | hsa_signal_store_relaxed /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp: In member function ‘bool roc::VirtualGPU::dispatchGenericAqlPacket(AqlPacket*, uint16_t, uint16_t, bool, size_t)’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:685:20: error: there are no arguments to ‘hsa_queue_add_write_index_screlease’ that depend on a template parameter, so a declaration of ‘hsa_queue_add_write_index_screlease’ must be available [-fpermissive] 685 | uint64_t index = hsa_queue_add_write_index_screlease(gpu_queue_, size); | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:696:19: error: there are no arguments to ‘hsa_queue_load_read_index_scacquire’ that depend on a template parameter, so a declaration of ‘hsa_queue_load_read_index_scacquire’ must be available [-fpermissive] 696 | while ((index - hsa_queue_load_read_index_scacquire(gpu_queue_)) >= queueMask) { | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/include/top.hpp:101, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/devhostcall.hpp:23, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:21: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:726:36: error: ‘HSA_PACKET_HEADER_SCACQUIRE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_ACQUIRE_FENCE_SCOPE’? 726 | extractAqlBits(header, HSA_PACKET_HEADER_SCACQUIRE_FENCE_SCOPE, | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:200:68: note: in definition of macro ‘ClPrint’ 200 | amd::log_printf(level, __FILENAME__, __LINE__, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:727:28: error: ‘HSA_PACKET_HEADER_WIDTH_SCACQUIRE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_WIDTH_ACQUIRE_FENCE_SCOPE’? 727 | HSA_PACKET_HEADER_WIDTH_SCACQUIRE_FENCE_SCOPE), | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:200:68: note: in definition of macro ‘ClPrint’ 200 | amd::log_printf(level, __FILENAME__, __LINE__, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:728:36: error: ‘HSA_PACKET_HEADER_SCRELEASE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_RELEASE_FENCE_SCOPE’? 728 | extractAqlBits(header, HSA_PACKET_HEADER_SCRELEASE_FENCE_SCOPE, | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:200:68: note: in definition of macro ‘ClPrint’ 200 | amd::log_printf(level, __FILENAME__, __LINE__, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:729:28: error: ‘HSA_PACKET_HEADER_WIDTH_SCRELEASE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_WIDTH_RELEASE_FENCE_SCOPE’? 729 | HSA_PACKET_HEADER_WIDTH_SCRELEASE_FENCE_SCOPE), | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:200:68: note: in definition of macro ‘ClPrint’ 200 | amd::log_printf(level, __FILENAME__, __LINE__, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:726:36: error: ‘HSA_PACKET_HEADER_SCACQUIRE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_ACQUIRE_FENCE_SCOPE’? 726 | extractAqlBits(header, HSA_PACKET_HEADER_SCACQUIRE_FENCE_SCOPE, | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:202:51: note: in definition of macro ‘ClPrint’ 202 | amd::log_printf(level, "", 0, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:727:28: error: ‘HSA_PACKET_HEADER_WIDTH_SCACQUIRE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_WIDTH_ACQUIRE_FENCE_SCOPE’? 727 | HSA_PACKET_HEADER_WIDTH_SCACQUIRE_FENCE_SCOPE), | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:202:51: note: in definition of macro ‘ClPrint’ 202 | amd::log_printf(level, "", 0, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:728:36: error: ‘HSA_PACKET_HEADER_SCRELEASE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_RELEASE_FENCE_SCOPE’? 728 | extractAqlBits(header, HSA_PACKET_HEADER_SCRELEASE_FENCE_SCOPE, | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:202:51: note: in definition of macro ‘ClPrint’ 202 | amd::log_printf(level, "", 0, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:729:28: error: ‘HSA_PACKET_HEADER_WIDTH_SCRELEASE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_WIDTH_RELEASE_FENCE_SCOPE’? 729 | HSA_PACKET_HEADER_WIDTH_SCRELEASE_FENCE_SCOPE), | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:202:51: note: in definition of macro ‘ClPrint’ 202 | amd::log_printf(level, "", 0, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:744:3: error: there are no arguments to ‘hsa_signal_store_screlease’ that depend on a template parameter, so a declaration of ‘hsa_signal_store_screlease’ must be available [-fpermissive] 744 | hsa_signal_store_screlease(gpu_queue_->doorbell_signal, index - 1); | ^~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp: In member function ‘void roc::VirtualGPU::dispatchBarrierPacket(hsa_barrier_and_packet_t*, uint16_t, bool)’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:813:20: error: ‘hsa_queue_add_write_index_screlease’ was not declared in this scope; did you mean ‘hsa_queue_add_write_index_release’? 813 | uint64_t index = hsa_queue_add_write_index_screlease(gpu_queue_, 1); | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ | hsa_queue_add_write_index_release /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:828:19: error: ‘hsa_queue_load_read_index_scacquire’ was not declared in this scope; did you mean ‘hsa_queue_load_read_index_acquire’? 828 | while ((index - hsa_queue_load_read_index_scacquire(gpu_queue_)) >= queueMask); | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ | hsa_queue_load_read_index_acquire /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:834:3: error: ‘hsa_signal_store_screlease’ was not declared in this scope; did you mean ‘hsa_signal_store_release’? 834 | hsa_signal_store_screlease(gpu_queue_->doorbell_signal, index); | ^~~~~~~~~~~~~~~~~~~~~~~~~~ | hsa_signal_store_release In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/include/top.hpp:101, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/devhostcall.hpp:23, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:21: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:844:40: error: ‘HSA_PACKET_HEADER_SCACQUIRE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_ACQUIRE_FENCE_SCOPE’? 844 | extractAqlBits(packetHeader, HSA_PACKET_HEADER_SCACQUIRE_FENCE_SCOPE, | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:200:68: note: in definition of macro ‘ClPrint’ 200 | amd::log_printf(level, __FILENAME__, __LINE__, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:845:27: error: ‘HSA_PACKET_HEADER_WIDTH_SCACQUIRE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_WIDTH_ACQUIRE_FENCE_SCOPE’? 845 | HSA_PACKET_HEADER_WIDTH_SCACQUIRE_FENCE_SCOPE), | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:200:68: note: in definition of macro ‘ClPrint’ 200 | amd::log_printf(level, __FILENAME__, __LINE__, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:846:40: error: ‘HSA_PACKET_HEADER_SCRELEASE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_RELEASE_FENCE_SCOPE’? 846 | extractAqlBits(packetHeader, HSA_PACKET_HEADER_SCRELEASE_FENCE_SCOPE, | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:200:68: note: in definition of macro ‘ClPrint’ 200 | amd::log_printf(level, __FILENAME__, __LINE__, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:847:27: error: ‘HSA_PACKET_HEADER_WIDTH_SCRELEASE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_WIDTH_RELEASE_FENCE_SCOPE’? 847 | HSA_PACKET_HEADER_WIDTH_SCRELEASE_FENCE_SCOPE), | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:200:68: note: in definition of macro ‘ClPrint’ 200 | amd::log_printf(level, __FILENAME__, __LINE__, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:844:40: error: ‘HSA_PACKET_HEADER_SCACQUIRE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_ACQUIRE_FENCE_SCOPE’? 844 | extractAqlBits(packetHeader, HSA_PACKET_HEADER_SCACQUIRE_FENCE_SCOPE, | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:202:51: note: in definition of macro ‘ClPrint’ 202 | amd::log_printf(level, "", 0, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:845:27: error: ‘HSA_PACKET_HEADER_WIDTH_SCACQUIRE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_WIDTH_ACQUIRE_FENCE_SCOPE’? 845 | HSA_PACKET_HEADER_WIDTH_SCACQUIRE_FENCE_SCOPE), | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:202:51: note: in definition of macro ‘ClPrint’ 202 | amd::log_printf(level, "", 0, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:846:40: error: ‘HSA_PACKET_HEADER_SCRELEASE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_RELEASE_FENCE_SCOPE’? 846 | extractAqlBits(packetHeader, HSA_PACKET_HEADER_SCRELEASE_FENCE_SCOPE, | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:202:51: note: in definition of macro ‘ClPrint’ 202 | amd::log_printf(level, "", 0, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:847:27: error: ‘HSA_PACKET_HEADER_WIDTH_SCRELEASE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_WIDTH_RELEASE_FENCE_SCOPE’? 847 | HSA_PACKET_HEADER_WIDTH_SCRELEASE_FENCE_SCOPE), | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:202:51: note: in definition of macro ‘ClPrint’ 202 | amd::log_printf(level, "", 0, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp: In member function ‘void roc::VirtualGPU::dispatchBarrierValuePacket(const hsa_amd_barrier_value_packet_t*, hsa_amd_vendor_packet_header_t)’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:2088:20: error: ‘hsa_queue_add_write_index_screlease’ was not declared in this scope; did you mean ‘hsa_queue_add_write_index_release’? 2088 | uint64_t index = hsa_queue_add_write_index_screlease(gpu_queue_, 1); | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ | hsa_queue_add_write_index_release /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:2089:19: error: ‘hsa_queue_load_read_index_scacquire’ was not declared in this scope; did you mean ‘hsa_queue_load_read_index_acquire’? 2089 | while ((index - hsa_queue_load_read_index_scacquire(gpu_queue_)) >= queueMask) { | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ | hsa_queue_load_read_index_acquire /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:2098:3: error: ‘hsa_signal_store_screlease’ was not declared in this scope; did you mean ‘hsa_signal_store_release’? 2098 | hsa_signal_store_screlease(gpu_queue_->doorbell_signal, index); | ^~~~~~~~~~~~~~~~~~~~~~~~~~ | hsa_signal_store_release In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/include/top.hpp:101, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/devhostcall.hpp:23, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:21: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:2106:41: error: ‘HSA_PACKET_HEADER_SCACQUIRE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_ACQUIRE_FENCE_SCOPE’? 2106 | extractAqlBits(header.header, HSA_PACKET_HEADER_SCACQUIRE_FENCE_SCOPE, | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:200:68: note: in definition of macro ‘ClPrint’ 200 | amd::log_printf(level, __FILENAME__, __LINE__, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:2107:26: error: ‘HSA_PACKET_HEADER_WIDTH_SCACQUIRE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_WIDTH_ACQUIRE_FENCE_SCOPE’? 2107 | HSA_PACKET_HEADER_WIDTH_SCACQUIRE_FENCE_SCOPE), | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:200:68: note: in definition of macro ‘ClPrint’ 200 | amd::log_printf(level, __FILENAME__, __LINE__, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:2108:41: error: ‘HSA_PACKET_HEADER_SCRELEASE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_RELEASE_FENCE_SCOPE’? 2108 | extractAqlBits(header.header, HSA_PACKET_HEADER_SCRELEASE_FENCE_SCOPE, | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:200:68: note: in definition of macro ‘ClPrint’ 200 | amd::log_printf(level, __FILENAME__, __LINE__, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:2109:26: error: ‘HSA_PACKET_HEADER_WIDTH_SCRELEASE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_WIDTH_RELEASE_FENCE_SCOPE’? 2109 | HSA_PACKET_HEADER_WIDTH_SCRELEASE_FENCE_SCOPE), | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:200:68: note: in definition of macro ‘ClPrint’ 200 | amd::log_printf(level, __FILENAME__, __LINE__, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:2106:41: error: ‘HSA_PACKET_HEADER_SCACQUIRE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_ACQUIRE_FENCE_SCOPE’? 2106 | extractAqlBits(header.header, HSA_PACKET_HEADER_SCACQUIRE_FENCE_SCOPE, | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:202:51: note: in definition of macro ‘ClPrint’ 202 | amd::log_printf(level, "", 0, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:2107:26: error: ‘HSA_PACKET_HEADER_WIDTH_SCACQUIRE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_WIDTH_ACQUIRE_FENCE_SCOPE’? 2107 | HSA_PACKET_HEADER_WIDTH_SCACQUIRE_FENCE_SCOPE), | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:202:51: note: in definition of macro ‘ClPrint’ 202 | amd::log_printf(level, "", 0, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:2108:41: error: ‘HSA_PACKET_HEADER_SCRELEASE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_RELEASE_FENCE_SCOPE’? 2108 | extractAqlBits(header.header, HSA_PACKET_HEADER_SCRELEASE_FENCE_SCOPE, | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:202:51: note: in definition of macro ‘ClPrint’ 202 | amd::log_printf(level, "", 0, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:2109:26: error: ‘HSA_PACKET_HEADER_WIDTH_SCRELEASE_FENCE_SCOPE’ was not declared in this scope; did you mean ‘HSA_PACKET_HEADER_WIDTH_RELEASE_FENCE_SCOPE’? 2109 | HSA_PACKET_HEADER_WIDTH_SCRELEASE_FENCE_SCOPE), | ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/utils/debug.hpp:202:51: note: in definition of macro ‘ClPrint’ 202 | amd::log_printf(level, "", 0, format, ##__VA_ARGS__); \ | ^~~~~~~~~~~ In file included from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocdevice.hpp:38, from /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:22: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp: In instantiation of ‘bool roc::WaitForSignal(hsa_signal_t) [with long unsigned int wait_time = 0; hsa_signal_t = hsa_signal_s]’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:119:34: required from here /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:62:34: error: ‘hsa_signal_wait_scacquire’ was not declared in this scope; did you mean ‘hsa_signal_wait_acquire’? 62 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ 63 | wait_time, HSA_WAIT_STATE_ACTIVE) != 0) { | ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:70:34: error: ‘hsa_signal_wait_scacquire’ was not declared in this scope; did you mean ‘hsa_signal_wait_acquire’? 70 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ 71 | timeout, HSA_WAIT_STATE_ACTIVE) != 0) { | ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:73:36: error: ‘hsa_signal_wait_scacquire’ was not declared in this scope, and no declarations were found by argument-dependent lookup at the point of instantiation [-fpermissive] 73 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ 74 | kUnlimitedWait, HSA_WAIT_STATE_BLOCKED) != 0) { | ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp: In instantiation of ‘bool roc::WaitForSignal(hsa_signal_t) [with long unsigned int wait_time = 50000; hsa_signal_t = hsa_signal_s]’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:392:60: required from here /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:62:34: error: ‘hsa_signal_wait_scacquire’ was not declared in this scope; did you mean ‘hsa_signal_wait_acquire’? 62 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ 63 | wait_time, HSA_WAIT_STATE_ACTIVE) != 0) { | ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:70:34: error: ‘hsa_signal_wait_scacquire’ was not declared in this scope; did you mean ‘hsa_signal_wait_acquire’? 70 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ 71 | timeout, HSA_WAIT_STATE_ACTIVE) != 0) { | ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.hpp:73:36: error: ‘hsa_signal_wait_scacquire’ was not declared in this scope, and no declarations were found by argument-dependent lookup at the point of instantiation [-fpermissive] 73 | if (hsa_signal_wait_scacquire(signal, HSA_SIGNAL_CONDITION_LT, kInitSignalValueOne, | ~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ 74 | kUnlimitedWait, HSA_WAIT_STATE_BLOCKED) != 0) { | ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp: In instantiation of ‘bool roc::VirtualGPU::dispatchGenericAqlPacket(AqlPacket*, uint16_t, uint16_t, bool, size_t) [with AqlPacket = hsa_kernel_dispatch_packet_s; uint16_t = short unsigned int; size_t = long unsigned int]’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:770:65: required from here /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:685:55: error: ‘hsa_queue_add_write_index_screlease’ was not declared in this scope; did you mean ‘hsa_queue_add_write_index_release’? 685 | uint64_t index = hsa_queue_add_write_index_screlease(gpu_queue_, size); | ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~~~~~~~~~~ | hsa_queue_add_write_index_release /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:696:54: error: ‘hsa_queue_load_read_index_scacquire’ was not declared in this scope; did you mean ‘hsa_queue_load_read_index_acquire’? 696 | while ((index - hsa_queue_load_read_index_scacquire(gpu_queue_)) >= queueMask) { | ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~~~~ | hsa_queue_load_read_index_acquire /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:744:29: error: ‘hsa_signal_store_screlease’ was not declared in this scope; did you mean ‘hsa_signal_store_release’? 744 | hsa_signal_store_screlease(gpu_queue_->doorbell_signal, index - 1); | ~~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ | hsa_signal_store_release /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp: In instantiation of ‘bool roc::VirtualGPU::dispatchGenericAqlPacket(AqlPacket*, uint16_t, uint16_t, bool, size_t) [with AqlPacket = hsa_barrier_and_packet_s; uint16_t = short unsigned int; size_t = long unsigned int]’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:776:65: required from here /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:685:55: error: ‘hsa_queue_add_write_index_screlease’ was not declared in this scope; did you mean ‘hsa_queue_add_write_index_release’? 685 | uint64_t index = hsa_queue_add_write_index_screlease(gpu_queue_, size); | ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~~~~~~~~~~ | hsa_queue_add_write_index_release /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:696:54: error: ‘hsa_queue_load_read_index_scacquire’ was not declared in this scope; did you mean ‘hsa_queue_load_read_index_acquire’? 696 | while ((index - hsa_queue_load_read_index_scacquire(gpu_queue_)) >= queueMask) { | ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~~~~ | hsa_queue_load_read_index_acquire /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:744:29: error: ‘hsa_signal_store_screlease’ was not declared in this scope; did you mean ‘hsa_signal_store_release’? 744 | hsa_signal_store_screlease(gpu_queue_->doorbell_signal, index - 1); | ~~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ | hsa_signal_store_release /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp: In instantiation of ‘bool roc::VirtualGPU::dispatchGenericAqlPacket(AqlPacket*, uint16_t, uint16_t, bool, size_t) [with AqlPacket = hsa_ext_amd_aql_pm4_packet_t; uint16_t = short unsigned int; size_t = long unsigned int]’: /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:793:90: required from here /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:685:55: error: ‘hsa_queue_add_write_index_screlease’ was not declared in this scope; did you mean ‘hsa_queue_add_write_index_release’? 685 | uint64_t index = hsa_queue_add_write_index_screlease(gpu_queue_, size); | ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~~~~~~~~~~ | hsa_queue_add_write_index_release /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:696:54: error: ‘hsa_queue_load_read_index_scacquire’ was not declared in this scope; did you mean ‘hsa_queue_load_read_index_acquire’? 696 | while ((index - hsa_queue_load_read_index_scacquire(gpu_queue_)) >= queueMask) { | ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~~~~ | hsa_queue_load_read_index_acquire /home/ian/Documents/rocm-build/ROCm/ROCclr/device/rocm/rocvirtual.cpp:744:29: error: ‘hsa_signal_store_screlease’ was not declared in this scope; did you mean ‘hsa_signal_store_release’? 744 | hsa_signal_store_screlease(gpu_queue_->doorbell_signal, index - 1); | ~~~~~~~~~~~~~~~~~~~~~~~~~~^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ | hsa_signal_store_release ninja: build stopped: subcommand failed.How to reproduce
bash 18.rocclr.sh