[hip-runtime-amd] HSA_AMD_AGENT_INFO_SVM_DIRECT_HOST_ACCESS not declared #704

SilverLuke · 2021-11-15T09:23:21Z

SilverLuke
Nov 15, 2021

I get this error in hip-runtime-amd when installing rocm-hip-sdk and rocm-opencl-sdk:

In member function ‘bool roc::Device::populateOCLDeviceConstants()’:
/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocdevice.cpp:1571:37: error: ‘HSA_AMD_AGENT_INFO_SVM_DIRECT_HOST_ACCESS’ was not declared in this scope

Full cmake build log

-- The C compiler identification is GNU 11.1.0
-- The CXX compiler identification is GNU 11.1.0
-- Detecting C compiler ABI info
-- Detecting C compiler ABI info - done
-- Check for working C compiler: /usr/bin/cc - skipped
-- Detecting C compile features
-- Detecting C compile features - done
-- Detecting CXX compiler ABI info
-- Detecting CXX compiler ABI info - done
-- Check for working CXX compiler: /usr/bin/c++ - skipped
-- Detecting CXX compile features
-- Detecting CXX compile features - done
-- HIP_COMMON_DIR found at /dati/luca/aur/hip-runtime-amd/src/HIP-rocm-4.5.0
-- Found Perl: /usr/bin/perl (found version "5.34.0") 
-- Found Git: /usr/bin/git (found version "2.33.1") 
-- Using CPACK_DEBIAN_PACKAGE_RELEASE local
-- CPACK_RPM_PACKAGE_RELEASE: local
-- HIP Platform: amd
-- HIP Runtime: rocclr
-- HIP Compiler: clang
-- HIP will be installed in: /opt/rocm/hip
-- ROCM Installation path(ROCM_PATH): /opt/rocm
-- Found ROCclr: /dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/include  
-- 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 AMD_OPENCL: /dati/luca/aur/hip-runtime-amd/src/ROCm-OpenCL-Runtime-rocm-4.5.0/khronos/headers/opencl2.2/CL  
-- Found NUMA: /usr/lib/libnuma.so  
-- Found ZLIB: /usr/lib/libz.so (found version "1.2.11") 
-- Found LibXml2: /usr/lib/libxml2.so (found version "2.9.12") 
'sh' '-c' '/dati/luca/aur/hip-runtime-amd/src/HIP-rocm-4.5.0/bin/hip_embed_pch.sh /dati/luca/aur/hip-runtime-amd/src/HIP-rocm-4.5.0/include /dati/luca/aur/hip-runtime-amd/src/build/include /dati/luca/aur/hip-runtime-amd/src/hipamd-rocm-4.5.0/include /usr/lib64/cmake/llvm/../../..'
+ /usr/lib64/cmake/llvm/../../../bin/clang -O3 --rocm-path=/dati/luca/aur/hip-runtime-amd/src/build/include/.. -std=c++17 -nogpulib -isystem /dati/luca/aur/hip-runtime-amd/src/build/include -isystem /dati/luca/aur/hip-runtime-amd/src/HIP-rocm-4.5.0/include -isystem /dati/luca/aur/hip-runtime-amd/src/hipamd-rocm-4.5.0/include --cuda-device-only -x hip /tmp/hip_pch.20736/hip_pch.h -E
+ cat /tmp/hip_pch.20736/hip_macros.h
+ /usr/lib64/cmake/llvm/../../../bin/clang -cc1 -O3 -emit-pch -triple amdgcn-amd-amdhsa -aux-triple x86_64-unknown-linux-gnu -fcuda-is-device -std=c++17 -fgnuc-version=4.2.1 -o /tmp/hip_pch.20736/hip.pch -x hip-cpp-output -
+ /usr/lib64/cmake/llvm/../../../bin/llvm-mc -o hip_pch.o /tmp/hip_pch.20736/hip_pch.mcin --filetype=obj
+ rm -rf /tmp/hip_pch.20736
-- HIP RTC enabled.
-- Configuring done
-- Generating done
-- Build files have been written to: /dati/luca/aur/hip-runtime-amd/src/build
[  1%] Generating hip_rtc_gen/hipRTC
[  2%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/comgrctx.cpp.o
[  6%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/appprofile.cpp.o
[  6%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/compiler/lib/utils/options.cpp.o
[  6%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/blit.cpp.o
[  7%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/blitcl.cpp.o
[  8%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/devhcmessages.cpp.o
[ 10%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/devhcprintf.cpp.o
[ 11%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/devhostcall.cpp.o
-- Appending hiprtc macros to /dati/luca/aur/hip-runtime-amd/src/build/src/hip_rtc_gen/hipRTC.
[ 12%] Generating hip_rtc_gen/hipRTC_header.o
[ 13%] Linking CXX shared library ../lib/libhiprtc-builtins.so
[ 13%] Built target hiprtc-builtins
[ 15%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/device.cpp.o
[ 16%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/devkernel.cpp.o
[ 17%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/devprogram.cpp.o
[ 18%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/devwavelimiter.cpp.o
[ 20%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/hsailctx.cpp.o
[ 21%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/hwdebug.cpp.o
[ 22%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/elf/elf.cpp.o
[ 24%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/os/alloc.cpp.o
[ 25%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/os/os_posix.cpp.o
[ 26%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/os/os_win32.cpp.o
[ 27%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/os/os.cpp.o
[ 29%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/platform/activity.cpp.o
[ 30%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/platform/agent.cpp.o
[ 31%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/platform/command.cpp.o
[ 32%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/platform/commandqueue.cpp.o
[ 34%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/platform/context.cpp.o
[ 35%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/platform/kernel.cpp.o
[ 36%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/platform/memory.cpp.o
[ 37%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/platform/ndrange.cpp.o
[ 39%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/platform/program.cpp.o
[ 40%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/platform/runtime.cpp.o
[ 41%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/thread/monitor.cpp.o
[ 43%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/thread/semaphore.cpp.o
[ 44%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/thread/thread.cpp.o
[ 45%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/utils/debug.cpp.o
[ 46%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/utils/flags.cpp.o
[ 48%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocappprofile.cpp.o
[ 49%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocblit.cpp.o
[ 50%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/roccounters.cpp.o
[ 51%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocdevice.cpp.o
[ 53%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocglinterop.cpp.o
[ 54%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rockernel.cpp.o
/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocdevice.cpp: In member function ‘bool roc::Device::populateOCLDeviceConstants()’:
/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocdevice.cpp:1571:37: error: ‘HSA_AMD_AGENT_INFO_SVM_DIRECT_HOST_ACCESS’ was not declared in this scope
 1571 |       static_cast<hsa_agent_info_t>(HSA_AMD_AGENT_INFO_SVM_DIRECT_HOST_ACCESS),
      |                                     ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocdevice.cpp: In member function ‘bool roc::Device::SetSvmAttributesInt(const void*, size_t, amd::MemoryAdvice, bool, bool) const’:
/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocdevice.cpp:2241:25: error: ‘HSA_AMD_SVM_ATTRIB_READ_MOSTLY’ was not declared in this scope; did you mean ‘HSA_AMD_SVM_ATTRIB_READ_ONLY’?
 2241 |         attr.push_back({HSA_AMD_SVM_ATTRIB_READ_MOSTLY, true});
      |                         ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
      |                         HSA_AMD_SVM_ATTRIB_READ_ONLY
/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocdevice.cpp:2241:23: error: no matching function for call to ‘std::vector<hsa_amd_svm_attribute_pair_s>::push_back(<brace-enclosed initializer list>)’
 2241 |         attr.push_back({HSA_AMD_SVM_ATTRIB_READ_MOSTLY, true});
      |         ~~~~~~~~~~~~~~^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
In file included from /usr/include/c++/11.1.0/vector:67,
                 from /dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/cmake/../os/os.hpp:27,
                 from /dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/cmake/../thread/thread.hpp:26,
                 from /dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/cmake/../device/device.hpp:25,
                 from /dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/cmake/../platform/program.hpp:32,
                 from /dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocdevice.cpp:23:
/usr/include/c++/11.1.0/bits/stl_vector.h:1187:7: note: candidate: ‘void std::vector<_Tp, _Alloc>::push_back(const value_type&) [with _Tp = hsa_amd_svm_attribute_pair_s; _Alloc = std::allocator<hsa_amd_svm_attribute_pair_s>; std::vector<_Tp, _Alloc>::value_type = hsa_amd_svm_attribute_pair_s]’
 1187 |       push_back(const value_type& __x)
      |       ^~~~~~~~~
/usr/include/c++/11.1.0/bits/stl_vector.h:1187:35: note:   no known conversion for argument 1 from ‘<brace-enclosed initializer list>’ to ‘const value_type&’ {aka ‘const hsa_amd_svm_attribute_pair_s&’}
 1187 |       push_back(const value_type& __x)
      |                 ~~~~~~~~~~~~~~~~~~^~~
/usr/include/c++/11.1.0/bits/stl_vector.h:1203:7: note: candidate: ‘void std::vector<_Tp, _Alloc>::push_back(std::vector<_Tp, _Alloc>::value_type&&) [with _Tp = hsa_amd_svm_attribute_pair_s; _Alloc = std::allocator<hsa_amd_svm_attribute_pair_s>; std::vector<_Tp, _Alloc>::value_type = hsa_amd_svm_attribute_pair_s]’
 1203 |       push_back(value_type&& __x)
      |       ^~~~~~~~~
/usr/include/c++/11.1.0/bits/stl_vector.h:1203:30: note:   no known conversion for argument 1 from ‘<brace-enclosed initializer list>’ to ‘std::vector<hsa_amd_svm_attribute_pair_s>::value_type&&’ {aka ‘hsa_amd_svm_attribute_pair_s&&’}
 1203 |       push_back(value_type&& __x)
      |                 ~~~~~~~~~~~~~^~~
/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocdevice.cpp:2244:23: error: no matching function for call to ‘std::vector<hsa_amd_svm_attribute_pair_s>::push_back(<brace-enclosed initializer list>)’
 2244 |         attr.push_back({HSA_AMD_SVM_ATTRIB_READ_MOSTLY, false});
      |         ~~~~~~~~~~~~~~^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
In file included from /usr/include/c++/11.1.0/vector:67,
                 from /dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/cmake/../os/os.hpp:27,
                 from /dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/cmake/../thread/thread.hpp:26,
                 from /dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/cmake/../device/device.hpp:25,
                 from /dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/cmake/../platform/program.hpp:32,
                 from /dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocdevice.cpp:23:
/usr/include/c++/11.1.0/bits/stl_vector.h:1187:7: note: candidate: ‘void std::vector<_Tp, _Alloc>::push_back(const value_type&) [with _Tp = hsa_amd_svm_attribute_pair_s; _Alloc = std::allocator<hsa_amd_svm_attribute_pair_s>; std::vector<_Tp, _Alloc>::value_type = hsa_amd_svm_attribute_pair_s]’
 1187 |       push_back(const value_type& __x)
      |       ^~~~~~~~~
/usr/include/c++/11.1.0/bits/stl_vector.h:1187:35: note:   no known conversion for argument 1 from ‘<brace-enclosed initializer list>’ to ‘const value_type&’ {aka ‘const hsa_amd_svm_attribute_pair_s&’}
 1187 |       push_back(const value_type& __x)
      |                 ~~~~~~~~~~~~~~~~~~^~~
/usr/include/c++/11.1.0/bits/stl_vector.h:1203:7: note: candidate: ‘void std::vector<_Tp, _Alloc>::push_back(std::vector<_Tp, _Alloc>::value_type&&) [with _Tp = hsa_amd_svm_attribute_pair_s; _Alloc = std::allocator<hsa_amd_svm_attribute_pair_s>; std::vector<_Tp, _Alloc>::value_type = hsa_amd_svm_attribute_pair_s]’
 1203 |       push_back(value_type&& __x)
      |       ^~~~~~~~~
/usr/include/c++/11.1.0/bits/stl_vector.h:1203:30: note:   no known conversion for argument 1 from ‘<brace-enclosed initializer list>’ to ‘std::vector<hsa_amd_svm_attribute_pair_s>::value_type&&’ {aka ‘hsa_amd_svm_attribute_pair_s&&’}
 1203 |       push_back(value_type&& __x)
      |                 ~~~~~~~~~~~~~^~~
/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocdevice.cpp: In member function ‘virtual bool roc::Device::GetSvmAttributes(void**, size_t*, int*, size_t, const void*, size_t) const’:
/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocdevice.cpp:2340:22: error: ‘hsa_amd_pointer_info_t’ {aka ‘struct hsa_amd_pointer_info_s’} has no member named ‘global_flags’
 2340 |         if (ptr_info.global_flags & HSA_AMD_MEMORY_POOL_GLOBAL_FLAG_COARSE_GRAINED) {
      |                      ^~~~~~~~~~~~
/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocdevice.cpp:2342:29: error: ‘hsa_amd_pointer_info_t’ {aka ‘struct hsa_amd_pointer_info_s’} has no member named ‘global_flags’
 2342 |         } else if (ptr_info.global_flags & HSA_AMD_MEMORY_POOL_GLOBAL_FLAG_FINE_GRAINED) {
      |                             ^~~~~~~~~~~~
[ 55%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocmemory.cpp.o
/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocdevice.cpp:2356:27: error: ‘HSA_AMD_SVM_ATTRIB_READ_MOSTLY’ was not declared in this scope; did you mean ‘HSA_AMD_SVM_ATTRIB_READ_ONLY’?
 2356 |           attr.push_back({HSA_AMD_SVM_ATTRIB_READ_MOSTLY, 0});
      |                           ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
      |                           HSA_AMD_SVM_ATTRIB_READ_ONLY
/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocdevice.cpp:2356:25: error: no matching function for call to ‘std::vector<hsa_amd_svm_attribute_pair_s>::push_back(<brace-enclosed initializer list>)’
 2356 |           attr.push_back({HSA_AMD_SVM_ATTRIB_READ_MOSTLY, 0});
      |           ~~~~~~~~~~~~~~^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
In file included from /usr/include/c++/11.1.0/vector:67,
                 from /dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/cmake/../os/os.hpp:27,
                 from /dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/cmake/../thread/thread.hpp:26,
                 from /dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/cmake/../device/device.hpp:25,
                 from /dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/cmake/../platform/program.hpp:32,
                 from /dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocdevice.cpp:23:
/usr/include/c++/11.1.0/bits/stl_vector.h:1187:7: note: candidate: ‘void std::vector<_Tp, _Alloc>::push_back(const value_type&) [with _Tp = hsa_amd_svm_attribute_pair_s; _Alloc = std::allocator<hsa_amd_svm_attribute_pair_s>; std::vector<_Tp, _Alloc>::value_type = hsa_amd_svm_attribute_pair_s]’
 1187 |       push_back(const value_type& __x)
      |       ^~~~~~~~~
/usr/include/c++/11.1.0/bits/stl_vector.h:1187:35: note:   no known conversion for argument 1 from ‘<brace-enclosed initializer list>’ to ‘const value_type&’ {aka ‘const hsa_amd_svm_attribute_pair_s&’}
 1187 |       push_back(const value_type& __x)
      |                 ~~~~~~~~~~~~~~~~~~^~~
/usr/include/c++/11.1.0/bits/stl_vector.h:1203:7: note: candidate: ‘void std::vector<_Tp, _Alloc>::push_back(std::vector<_Tp, _Alloc>::value_type&&) [with _Tp = hsa_amd_svm_attribute_pair_s; _Alloc = std::allocator<hsa_amd_svm_attribute_pair_s>; std::vector<_Tp, _Alloc>::value_type = hsa_amd_svm_attribute_pair_s]’
 1203 |       push_back(value_type&& __x)
      |       ^~~~~~~~~
/usr/include/c++/11.1.0/bits/stl_vector.h:1203:30: note:   no known conversion for argument 1 from ‘<brace-enclosed initializer list>’ to ‘std::vector<hsa_amd_svm_attribute_pair_s>::value_type&&’ {aka ‘hsa_amd_svm_attribute_pair_s&&’}
 1203 |       push_back(value_type&& __x)
      |                 ~~~~~~~~~~~~~^~~
[ 56%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocprintf.cpp.o
[ 58%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocprogram.cpp.o
[ 59%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocschedcl.cpp.o
[ 60%] Building CXX object src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocsettings.cpp.o
make[2]: *** [src/CMakeFiles/rocclr.dir/build.make:594: src/CMakeFiles/rocclr.dir/dati/luca/aur/hip-runtime-amd/src/ROCclr-rocm-4.5.0/device/rocm/rocdevice.cpp.o]

Answered by tpkessler

Nov 19, 2021

Ok, you still have ROCm 4.3.1 installed. To update to 4.5.0, you have to first remove all ROCm packages, see the README of this repo.

View full answer

tpkessler · 2021-11-16T07:38:04Z

tpkessler
Nov 16, 2021
Maintainer

Did you uninstall all old ROCm packages before building 4.5.0?

0 replies

SilverLuke · 2021-11-16T11:38:30Z

SilverLuke
Nov 16, 2021
Author

I have tried some time ago installing rocm for tensorflow-rocm with no luck (I ended up uninstalling everything rocm related with yay -Rcs rocm-... but I do not remember well). I currently have only the opencl-amd package and when I run yay -S rocm-hip-sdk rocm-opencl-sdk I always say cleanBuild all and then yay ask for uninstalling opencl-amd where I answer yes.
I have tried to uninstall yay -Rcs opencl-amd opencl-clhpp opencl-headers first and then installing rocm following the guide but I get the same error.

P.S. My current system is:

GPU: RX 580 8GB, Device Name Ellesmere (It should be a gfx803)
CPU: AMD Ryzen 5 3400G with Radeon Vega Graphics (Should be gfx902:xnack+ and should not work)
Linux: 5.15.2-arch1-1

There is a simple way to get the gfx naming?

0 replies

tpkessler · 2021-11-19T16:14:48Z

tpkessler
Nov 19, 2021
Maintainer

uninstalling everything rocm related

What's the output of

pacman -Qqo /opt/rocm

There is a simple way to get the gfx naming?

Call rocminfo.

0 replies

SilverLuke · 2021-11-19T16:55:17Z

SilverLuke
Nov 19, 2021
Author

Output of pacman -Qqo /opt/rocm:

comgr
hip-rocclr
hipblas
hipcub
hipfft
hipsparse
hsa-rocr
hsakmt-roct
llvm-amdgpu
rccl
rocalution
rocblas
rocclr
rocfft
rocm-cmake
rocm-core
rocm-device-libs
rocm-language-runtime
rocminfo
rocprim
rocrand
rocsolver
rocsparse
rocthrust

0 replies

tpkessler · 2021-11-19T17:16:33Z

tpkessler
Nov 19, 2021
Maintainer

Ok, so you have the full ROCm stack installed. Could you please run

LANG=C pacman -Qo /opt/rocm

so that we can see the version of the installed packages?

0 replies

SilverLuke · 2021-11-19T17:26:06Z

SilverLuke
Nov 19, 2021
Author

/opt/rocm/ is owned by comgr 4.3.1-1
/opt/rocm/ is owned by hip-rocclr 4.3.1-1
/opt/rocm/ is owned by hipblas 4.3.1-1
/opt/rocm/ is owned by hipcub 4.3.1-1
/opt/rocm/ is owned by hipfft 4.2.0-1
/opt/rocm/ is owned by hipsparse 4.3.1-1
/opt/rocm/ is owned by hsa-rocr 4.3.1-1
/opt/rocm/ is owned by hsakmt-roct 4.5.0-1
/opt/rocm/ is owned by llvm-amdgpu 4.3.1-1
/opt/rocm/ is owned by rccl 4.3.1-1
/opt/rocm/ is owned by rocalution 4.3.1-1
/opt/rocm/ is owned by rocblas 4.3.1-1
/opt/rocm/ is owned by rocclr 4.3.1-1
/opt/rocm/ is owned by rocfft 4.2.0-1
/opt/rocm/ is owned by rocm-cmake 4.5.0-1
/opt/rocm/ is owned by rocm-core 4.5.0-1
/opt/rocm/ is owned by rocm-device-libs 4.3.1-1
/opt/rocm/ is owned by rocm-language-runtime 4.5.0-2
/opt/rocm/ is owned by rocm-opencl-runtime 4.3.1-1
/opt/rocm/ is owned by rocminfo 4.3.1-1
/opt/rocm/ is owned by rocprim 4.3.1-1
/opt/rocm/ is owned by rocrand 4.3.1-1
/opt/rocm/ is owned by rocsolver 4.3.1-1
/opt/rocm/ is owned by rocsparse 4.3.1-1
/opt/rocm/ is owned by rocthrust 4.3.1-1

0 replies

tpkessler · 2021-11-19T17:36:49Z

tpkessler
Nov 19, 2021
Maintainer

Ok, you still have ROCm 4.3.1 installed. To update to 4.5.0, you have to first remove all ROCm packages, see the README of this repo.

0 replies

SilverLuke · 2021-11-19T18:05:20Z

SilverLuke
Nov 19, 2021
Author

After I run pacman -Rcs comgr hip-rocclr hipblas hipcub hipfft hipsparse hsa-rocr hsakmt-roct llvm-amdgpu rccl rocalution rocblas rocclr rocfft rocm-cmake rocm-core rocm-device-libs rocm-language-runtime rocminfo rocprim rocrand rocsolver rocsparse rocthrust the /opt/rocm folder is gone, so I have uninstalled rocm, after that I run yay -S rocm-hip-sdk rocm-opencl-sdk but I get the same error and with some package I have the correct version but in other don't.
I use the arch4edu repository.

0 replies

tpkessler · 2021-11-19T18:12:26Z

tpkessler
Nov 19, 2021
Maintainer

I use the arch4edu repository.

Oh! I think it's not fully synced yet. You either build everything from source now or wait for the packages to be updated in arch4edu.

0 replies

tpkessler · 2022-02-12T09:43:24Z

tpkessler
Feb 12, 2022
Maintainer

The package has been updated to 5.0.0. Could you please try to build hip again @SilverLuke?

0 replies

SilverLuke · 2022-02-14T21:31:24Z

SilverLuke
Feb 14, 2022
Author

I am following this issue and seem the support for gfx800 is dropped or not working anymore, so I will wait some time before recompile ROCm.

0 replies

gururise · 2022-02-24T19:04:40Z

gururise
Feb 24, 2022

The package has been updated to 5.0.0. Could you please try to build hip again @SilverLuke?

I tried updating (using arch4edu) just now (after completely uninstalling rocm), and I end up with this failure:

[ 40%] Building CXX object src/CMakeFiles/rocclr.dir/home/gene/.cache/yay/hip-runtime-amd/src/ROCclr-rocm-5.0.1/device/rocm/rocdevice.cpp.o
/home/gene/.cache/yay/hip-runtime-amd/src/ROCclr-rocm-5.0.1/device/rocm/rocdevice.cpp: In member function ‘bool roc::Device::populateOCLDeviceConstants()’:
/home/gene/.cache/yay/hip-runtime-amd/src/ROCclr-rocm-5.0.1/device/rocm/rocdevice.cpp:1079:44: error: ‘HSA_AMD_AGENT_INFO_COOPERATIVE_COMPUTE_UNIT_COUNT’ was not declared in this scope; did you mean ‘HSA_AMD_AGENT_INFO_COMPUTE_UNIT_COUNT’?
 1079 |                          (hsa_agent_info_t)HSA_AMD_AGENT_INFO_COOPERATIVE_COMPUTE_UNIT_COUNT,
      |                                            ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
      |                                            HSA_AMD_AGENT_INFO_COMPUTE_UNIT_COUNT
make[2]: *** [src/CMakeFiles/rocclr.dir/build.make:608: src/CMakeFiles/rocclr.dir/home/gene/.cache/yay/hip-runtime-amd/src/ROCclr-rocm-5.0.1/device/rocm/rocdevice.cpp.o] Error 1
make[1]: *** [CMakeFiles/Makefile2:10413: src/CMakeFiles/rocclr.dir/all] Error 2
make: *** [Makefile:146: all] Error 2
==> ERROR: A failure occurred in build().
    Aborting...
 -> error making: hip-runtime-amd

1 reply

acxz Jun 18, 2022
Maintainer

If you are still experiencing this issue @gururise please open another post. Marking this as solved since @SilverLuke (OP) has gotten past this issue.

acxz · 2022-03-28T07:03:39Z

acxz
Mar 28, 2022
Maintainer

@SilverLuke @gururise have been you able to try building from source instead of using the arch4edu binaries? We currently do not recommend them as they are out of sync. They might be slowing coming back to life: https://github.com/arch4edu/arch4edu/commits/master !!!!!!

I'll move this to discussions for now until we hear back from any of you two if you are able to reproduce this issue without using arch4edu.

0 replies

SilverLuke · 2022-06-18T07:34:28Z

SilverLuke
Jun 18, 2022
Author

Hello! I have changed the CPU on my pc so I cannot be able to test if this error keeps up.
Now I have a AMD Ryzen 9 5900X with ROCM 5.1.3, and them works well with my gfx803.

1 reply

acxz Jun 18, 2022
Maintainer

I'll take that as the solution was the update of the entire rocm stack. And for your specific case waiting for the gfx8** patch to be incorporated into our builds. thx for following up.

Provide feedback

Saved searches

Use saved searches to filter your results more quickly

rocm-arch

[hip-runtime-amd] HSA_AMD_AGENT_INFO_SVM_DIRECT_HOST_ACCESS not declared #704

{{title}}

Replies: 14 comments 2 replies

{{title}}

{{title}}

{{title}}

{{title}}

{{title}}

{{title}}

{{title}}

{{title}}

{{title}}

{{title}}

{{title}}

{{title}}

{{editor}}'s edit

{{editor}}'s edit

{{title}}

{{title}}

{{editor}}'s edit

{{editor}}'s edit

{{title}}

{{title}}

Select a reply

rocm-arch

[hip-runtime-amd] HSA_AMD_AGENT_INFO_SVM_DIRECT_HOST_ACCESS not declared #704

SilverLuke Nov 15, 2021

Replies: 14 comments · 2 replies

tpkessler Nov 16, 2021 Maintainer

SilverLuke Nov 16, 2021 Author

tpkessler Nov 19, 2021 Maintainer

SilverLuke Nov 19, 2021 Author

tpkessler Nov 19, 2021 Maintainer

SilverLuke Nov 19, 2021 Author

tpkessler Nov 19, 2021 Maintainer

SilverLuke Nov 19, 2021 Author

tpkessler Nov 19, 2021 Maintainer

tpkessler Feb 12, 2022 Maintainer

SilverLuke Feb 14, 2022 Author

gururise Feb 24, 2022

acxz Jun 18, 2022 Maintainer

acxz Mar 28, 2022 Maintainer

SilverLuke Jun 18, 2022 Author

acxz Jun 18, 2022 Maintainer

SilverLuke
Nov 15, 2021

Replies: 14 comments 2 replies

tpkessler
Nov 16, 2021
Maintainer

SilverLuke
Nov 16, 2021
Author

tpkessler
Nov 19, 2021
Maintainer

SilverLuke
Nov 19, 2021
Author

tpkessler
Nov 19, 2021
Maintainer

SilverLuke
Nov 19, 2021
Author

tpkessler
Nov 19, 2021
Maintainer

SilverLuke
Nov 19, 2021
Author

tpkessler
Nov 19, 2021
Maintainer

tpkessler
Feb 12, 2022
Maintainer

SilverLuke
Feb 14, 2022
Author

gururise
Feb 24, 2022

acxz Jun 18, 2022
Maintainer

acxz
Mar 28, 2022
Maintainer

SilverLuke
Jun 18, 2022
Author

acxz Jun 18, 2022
Maintainer