Bug#1118618: Updating rocr-runtime libraries to 6.4 causes llama.cpp/ggml to fail
Control: reassign -1 libamdhip64-5 5.7.1-6
On 2025-10-22 17:16, Cordell Bloor wrote:
The problem seems to be that upstream changed the ABI of
hsa_agent_iterate_isas by changing the types for the callback function
I was mistaken. I tried to fix the ABI breakage only to find nothing
there. AFAICT, the expected data layout for the callback function is
defined by the caller, not by libhsa-runtime64-1. I created a minimal
reproducer to compare the traced output when linked libamdhip64-5 and
libamdhip64-6.
$ cat main.hip
#include <hip/hip_runtime_api.h>
int main() {
float *dArr;
hipMalloc(&dArr, 1);
return 0;
}
$ clang++-21 main.hip -o hip5
$ apt install -t experimental libamdhip64-dev
$ clang++-21 main.hip -o hip6
$ ltrace -C -e "hsa*" -e "hip*" ./hip5 2> ltrace5.txt
$ ltrace -C -e "hsa*" -e "hip*" ./hip6 2> ltrace5.txt
The ltrace5.txt and ltrace6.txt logs are attached. The output indicates
the crash is in libamdhip64-5.
Enabling logging indicates that this is the fault of libamdhip64-5, as
it incorrectly assumes there cannot be more than one supported ISA for a
given device.
$ AMD_LOG_LEVEL=5 ./hip5
:3:rocdevice.cpp :442 : 102386455878 us: [pid:127063
tid:0x7fbecb179ac0] Initializing HSA stack.
:1:rocdevice.cpp :590 : 102386476567 us: [pid:127063
tid:0x7fbecb179ac0] HSA device gfx906 (PCI ID 66af) has 2 ISAs but can
only support a single ISA
:1:rocdevice.cpp :506 : 102386476578 us: [pid:127063
tid:0x7fbecb179ac0] Error creating new instance of Device.
free(): invalid pointer
Aborted AMD_LOG_LEVEL=5 ./hip5
This bad assumption was fixed in libamdhip64-6 6.4.3-1~exp2.
Sincerely,
Cory Bloor
hip5_a.out->hipMalloc(0x7ffcf0f0e480, 1, 0x7ffcf0f0e5b8, 0x560d2f54cd98 <unfinished ...>
libamdhip64.so.5->hsa_init(0, 0x7ffcf0f0de50, 0, 0x560d4920a <unfinished ...>
libhsa-runtime64.so.1->hsaKmtOpenKFD(0x7ffcf0f0db00, -8, 0x7f1cbb640040, 8) = 0
libhsa-runtime64.so.1->hsaKmtRuntimeEnable(0x7f1cbba00660, 0, 0, 0x560d49214 <unfinished ...>
libhsakmt.so.1->hsaKmtCheckRuntimeDebugSupport(0x7f1cbba00660, 0, 0, 0x560d49214 <unfinished ...>
libhsakmt.so.1->hsaKmtAcquireSystemProperties(0x7ffcf0f0d920, 0, 0, 0) = 0
libhsakmt.so.1->hsaKmtGetNodeProperties(0, 0x7ffcf0f0d930, 2, 0) = 0
libhsakmt.so.1->hsaKmtGetNodeProperties(1, 0x7ffcf0f0d930, 0, 0) = 0
libhsakmt.so.1->hsaKmtGetVersion(0x7ffcf0f0d918, 0, 0, 0x7f1cc19c4fff) = 0
<... hsaKmtCheckRuntimeDebugSupport resumed> ) = 0
<... hsaKmtRuntimeEnable resumed> ) = 0
libhsa-runtime64.so.1->hsaKmtGetRuntimeCapabilities(0x7ffcf0f0db24, 0xc0104b25, 0, 0) = 0
libhsa-runtime64.so.1->hsaKmtGetVersion(0x560d4920f5cc, 0xc0104b25, 0x560d4920ea60, 0) = 0
libhsa-runtime64.so.1->hsaKmtGetXNACKMode(0x7ffcf0f0db04, 0xc0104b25, 0x7f1cbff35158, 0x1200000001) = 0
libhsa-runtime64.so.1->hsaKmtReleaseSystemProperties(0x560d4920f5c0, 0x560d49214eec, 0x7ffcf0f0d930, 0x560d49214eec) = 0
libhsa-runtime64.so.1->hsaKmtAcquireSystemProperties(0x560d49214eec, 0, 0, 0x560829f5dc5f) = 0
libhsa-runtime64.so.1->hsaKmtGetNodeProperties(0, 0x7ffcf0f0d9e0, 0, 0) = 0
libhsa-runtime64.so.1->hsaKmtGetNodeMemoryProperties(0, 1, 0x560d49214650, 0x560d49214650) = 0
libhsa-runtime64.so.1->hsaKmtGetNodeCacheProperties(0, 0, 52, 0x560d4924a9b0) = 0
libhsa-runtime64.so.1->hsaKmtGetNodeProperties(1, 0x7ffcf0f0d9e0, 1, 0) = 0
libhsa-runtime64.so.1->hsaKmtGetNodeIoLinkProperties(1, 1, 0x560d49211cd0, 0x560d49211cd0) = 0
libhsa-runtime64.so.1->hsaKmtGetNodeProperties(1, 0x7ffcf0f0d610, 1, 1) = 0
libhsa-runtime64.so.1->hsaKmtGetClockCounters(1, 0x560d49212098, 2, 0) = 0
libhsa-runtime64.so.1->hsaKmtGetAMDGPUDeviceHandle(1, 0x7ffcf0f0d350, 128, 0x560d492325c8) = 0
libhsa-runtime64.so.1->hsaKmtGetNodeMemoryProperties(1, 5, 0x560d49238be0, 0x560d49238be0) = 0
libhsa-runtime64.so.1->hsaKmtGetNodeCacheProperties(1, 0x80001000, 109, 0x560d49258040) = 0
libhsa-runtime64.so.1->hsaKmtCreateEvent(0x7ffcf0f0db40, 1, 0, 0x7ffcf0f0db38 <unfinished ...>
libhsakmt.so.1->hsaKmtMapMemoryToGPU(0x7f1cc19b8000, 0x8000, 0x7ffcf0f0da58, 0) = 0
<... hsaKmtCreateEvent resumed> ) = 0
libhsa-runtime64.so.1->hsaKmtAllocMemory(0, 0x200000, 0x20040, 0x7ffcf0f0d920 <unfinished ...>
libhsakmt.so.1->hsaKmtAllocMemoryAlign(0, 0x200000, 0, 0x20040) = 0
<... hsaKmtAllocMemory resumed> ) = 0
libhsa-runtime64.so.1->hsaKmtMapMemoryToGPUNodes(0x7f1cb1e00000, 0x200000, 0x7ffcf0f0d920, 0) = 0
libhsa-runtime64.so.1->hsaKmtCreateEvent(0x7ffcf0f0da10, 0, 0, 0x7ffcf0f0da08) = 0
libhsa-runtime64.so.1->hsaKmtCreateEvent(0x7ffcf0f0db40, 1, 0, 0x7ffcf0f0db38) = 0
libhsa-runtime64.so.1->hsaKmtAllocMemory(1, 0x100000000, 576, 0x7ffcf0f0db50 <unfinished ...>
libhsakmt.so.1->hsaKmtAllocMemoryAlign(1, 0x100000000, 0, 576) = 0
<... hsaKmtAllocMemory resumed> ) = 0
libhsa-runtime64.so.1->hsaKmtAllocMemory(0, 4096, 0x21040, 0x7ffcf0f0d390 <unfinished ...>
libhsakmt.so.1->hsaKmtAllocMemoryAlign(0, 4096, 0, 0x21040) = 0
<... hsaKmtAllocMemory resumed> ) = 0
libhsa-runtime64.so.1->hsaKmtMapMemoryToGPUNodes(0x7f1cc19c2000, 4096, 0x7ffcf0f0d390, 0) = 0
libhsa-runtime64.so.1->hsaKmtSetTrapHandler(1, 0x7f1cc19c2000, 4096, 0) = 0
<... hsa_init resumed> ) = 0
libamdhip64.so.5->hsa_system_get_major_extension_table(513, 1, 24, 0x7f1cc180b780) = 0
libamdhip64.so.5->hsa_iterate_agents(0x7f1cc03deda0, 0, 0, 0x7f1cc180b788 <unfinished ...>
libamdhip64.so.5->hsa_agent_get_info(0x560d49214f10, 17, 0x7ffcf0f0db7c, 0x7f1cc180b788) = 0
libamdhip64.so.5->hsa_amd_agent_iterate_memory_pools(0x560d49214f10, 0x7f1cc03d5ee0, 0x7ffcf0f0db80, 0 <unfinished ...>
libamdhip64.so.5->hsa_amd_memory_pool_get_info(0x560d49214680, 0, 0x7ffcf0f0dab0, 0x7ffcf0f0db80) = 0
libamdhip64.so.5->hsa_amd_memory_pool_get_info(0x560d49214680, 1, 0x7ffcf0f0dab4, 0x7ffcf0f0dab0) = 0
libamdhip64.so.5->hsa_amd_memory_pool_get_info(0x560d49210650, 0, 0x7ffcf0f0dab0, 0x7ffcf0f0dab4) = 0
libamdhip64.so.5->hsa_amd_memory_pool_get_info(0x560d49210650, 1, 0x7ffcf0f0dab4, 0x7ffcf0f0dab0) = 0
libamdhip64.so.5->hsa_amd_memory_pool_get_info(0x560d49210a30, 0, 0x7ffcf0f0dab0, 0x7ffcf0f0dab4) = 0
libamdhip64.so.5->hsa_amd_memory_pool_get_info(0x560d49210a30, 1, 0x7ffcf0f0dab4, 0x7ffcf0f0dab0) = 0
libamdhip64.so.5->hsa_amd_memory_pool_get_info(0x560d49210e20, 0, 0x7ffcf0f0dab0, 0x7ffcf0f0dab4) = 0
libamdhip64.so.5->hsa_amd_memory_pool_get_info(0x560d49210e20, 1, 0x7ffcf0f0dab4, 0x7ffcf0f0dab0) = 0
<... hsa_amd_agent_iterate_memory_pools resumed> ) = 0
libamdhip64.so.5->hsa_agent_get_info(0x560d49211d10, 17, 0x7ffcf0f0db7c, 0) = 0
<... hsa_iterate_agents resumed> ) = 0
libamdhip64.so.5->hsa_agent_get_info(0x560d49211d10, 0, 0x7ffcf0f0dbc0, 0x560d4923cf38) = 0
libamdhip64.so.5->hsa_agent_get_info(0x560d49211d10, 0xa000, 0x560d49274850, 0x363039) = 0
libamdhip64.so.5->hsa_agent_iterate_isas(0x560d49211d10, 0x7f1cc03d5b40, 0x7ffcf0f0daf0, 0x560d49211d10) = 0
free(): invalid pointer
--- SIGABRT (Aborted) ---
+++ killed by SIGABRT +++
hip6_a.out->hipMalloc(0x7ffc4c23df70, 1, 0x7ffc4c23e0a8, 0x55a5e82bcd98 <unfinished ...>
libamdhip64.so.6->hsa_init(0, 0, 0x7fc0a445e380, 0x55a625f54 <unfinished ...>
libhsa-runtime64.so.1->hsaKmtOpenKFD(0x7ffc4c23d2c0, -8, 0x7fc0a3640040, 8) = 0
libhsa-runtime64.so.1->hsaKmtRuntimeEnable(0x7fc0a3a00660, 0, 0, 0x55a625f54 <unfinished ...>
libhsakmt.so.1->hsaKmtCheckRuntimeDebugSupport(0x7fc0a3a00660, 0, 0, 0x55a625f54 <unfinished ...>
libhsakmt.so.1->hsaKmtAcquireSystemProperties(0x7ffc4c23d0e0, 0, 0, 0) = 0
libhsakmt.so.1->hsaKmtGetNodeProperties(0, 0x7ffc4c23d0f0, 2, 0) = 0
libhsakmt.so.1->hsaKmtGetNodeProperties(1, 0x7ffc4c23d0f0, 0, 0) = 0
libhsakmt.so.1->hsaKmtGetVersion(0x7ffc4c23d0d8, 0, 0, 0x7fc0a5bb4fff) = 0
<... hsaKmtCheckRuntimeDebugSupport resumed> ) = 0
<... hsaKmtRuntimeEnable resumed> ) = 0
libhsa-runtime64.so.1->hsaKmtGetRuntimeCapabilities(0x7ffc4c23d2e4, 0xc0104b25, 0, 0) = 0
libhsa-runtime64.so.1->hsaKmtGetVersion(0x55a625f545fc, 0xc0104b25, 0x55a625f58900, 0) = 0
libhsa-runtime64.so.1->hsaKmtGetXNACKMode(0x7ffc4c23d2c4, 0xc0104b25, 0x7fc0a5a49158, 0x1200000001) = 0
libhsa-runtime64.so.1->hsaKmtReleaseSystemProperties(0x55a625f545f0, 0x55a625f5441c, 0x7ffc4c23d0f0, 0x55a625f5441c) = 0
libhsa-runtime64.so.1->hsaKmtAcquireSystemProperties(0x55a625f5441c, 0, 0, 0x55a37f971114) = 0
libhsa-runtime64.so.1->hsaKmtGetNodeProperties(0, 0x7ffc4c23d1a0, 0, 0) = 0
libhsa-runtime64.so.1->hsaKmtGetNodeMemoryProperties(0, 1, 0x55a625f5d290, 0x55a625f5d290) = 0
libhsa-runtime64.so.1->hsaKmtGetNodeCacheProperties(0, 0, 52, 0x55a625f93040) = 0
libhsa-runtime64.so.1->hsaKmtGetNodeProperties(1, 0x7ffc4c23d1a0, 1, 0) = 0
libhsa-runtime64.so.1->hsaKmtGetNodeIoLinkProperties(1, 1, 0x55a625f5b650, 0x55a625f5b650) = 0
libhsa-runtime64.so.1->hsaKmtGetNodeProperties(1, 0x7ffc4c23cdd0, 1, 1) = 0
libhsa-runtime64.so.1->hsaKmtGetClockCounters(1, 0x55a625f5ba18, 2, 0) = 0
libhsa-runtime64.so.1->hsaKmtGetAMDGPUDeviceHandle(1, 0x7ffc4c23cb10, 128, 0x55a625f7bc78) = 0
libhsa-runtime64.so.1->hsaKmtGetNodeMemoryProperties(1, 5, 0x55a625f82200, 0x55a625f82200) = 0
libhsa-runtime64.so.1->hsaKmtGetNodeCacheProperties(1, 0x80001000, 109, 0x55a625fa06d0) = 0
libhsa-runtime64.so.1->hsaKmtCreateEvent(0x7ffc4c23d300, 1, 0, 0x7ffc4c23d2f8 <unfinished ...>
libhsakmt.so.1->hsaKmtMapMemoryToGPU(0x7fc0a5ba8000, 0x8000, 0x7ffc4c23d218, 0) = 0
<... hsaKmtCreateEvent resumed> ) = 0
libhsa-runtime64.so.1->hsaKmtAllocMemory(0, 0x200000, 0x20040, 0x7ffc4c23d0e0 <unfinished ...>
libhsakmt.so.1->hsaKmtAllocMemoryAlign(0, 0x200000, 0, 0x20040) = 0
<... hsaKmtAllocMemory resumed> ) = 0
libhsa-runtime64.so.1->hsaKmtMapMemoryToGPUNodes(0x7fc0a3200000, 0x200000, 0x7ffc4c23d0e0, 0) = 0
libhsa-runtime64.so.1->hsaKmtCreateEvent(0x7ffc4c23d1d0, 0, 0, 0x7ffc4c23d1c8) = 0
libhsa-runtime64.so.1->hsaKmtCreateEvent(0x7ffc4c23d300, 1, 0, 0x7ffc4c23d2f8) = 0
libhsa-runtime64.so.1->hsaKmtAllocMemory(1, 0x100000000, 576, 0x7ffc4c23d310 <unfinished ...>
libhsakmt.so.1->hsaKmtAllocMemoryAlign(1, 0x100000000, 0, 576) = 0
<... hsaKmtAllocMemory resumed> ) = 0
libhsa-runtime64.so.1->hsaKmtAllocMemory(0, 4096, 0x21040, 0x7ffc4c23cb50 <unfinished ...>
libhsakmt.so.1->hsaKmtAllocMemoryAlign(0, 4096, 0, 0x21040) = 0
<... hsaKmtAllocMemory resumed> ) = 0
libhsa-runtime64.so.1->hsaKmtMapMemoryToGPUNodes(0x7fc0a5bb2000, 4096, 0x7ffc4c23cb50, 0) = 0
libhsa-runtime64.so.1->hsaKmtSetTrapHandler(1, 0x7fc0a5bb2000, 4096, 0) = 0
<... hsa_init resumed> ) = 0
libamdhip64.so.6->hsa_system_get_major_extension_table(513, 1, 24, 0x7fc0a59a9e90) = 0
libamdhip64.so.6->hsa_iterate_agents(0x7fc0a4423ac0, 0, 0, 0x7fc0a59a9e98 <unfinished ...>
libamdhip64.so.6->hsa_agent_get_info(0x55a625f40bd0, 17, 0x7ffc4c23d33c, 0x7fc0a59a9e98) = 0
libamdhip64.so.6->hsa_amd_agent_iterate_memory_pools(0x55a625f40bd0, 0x7fc0a441b760, 0x7ffc4c23d340, 0x7fc0a3763574 <unfinished ...>
libamdhip64.so.6->hsa_amd_memory_pool_get_info(0x55a625f596e0, 0, 0x7ffc4c23d270, 0x7ffc4c23d340) = 0
libamdhip64.so.6->hsa_amd_memory_pool_get_info(0x55a625f596e0, 1, 0x7ffc4c23d274, 0x7ffc4c23d270) = 0
libamdhip64.so.6->hsa_amd_memory_pool_get_info(0x55a625f59a50, 0, 0x7ffc4c23d270, 0x7ffc4c23d274) = 0
libamdhip64.so.6->hsa_amd_memory_pool_get_info(0x55a625f59a50, 1, 0x7ffc4c23d274, 0x7ffc4c23d270) = 0
libamdhip64.so.6->hsa_amd_memory_pool_get_info(0x55a625f5a490, 0, 0x7ffc4c23d270, 0x7ffc4c23d274) = 0
libamdhip64.so.6->hsa_amd_memory_pool_get_info(0x55a625f5a490, 1, 0x7ffc4c23d274, 0x7ffc4c23d270) = 0
libamdhip64.so.6->hsa_amd_memory_pool_get_info(0x55a625f5a880, 0, 0x7ffc4c23d270, 0x7ffc4c23d274) = 0
libamdhip64.so.6->hsa_amd_memory_pool_get_info(0x55a625f5a880, 1, 0x7ffc4c23d274, 0x7ffc4c23d270) = 0
<... hsa_amd_agent_iterate_memory_pools resumed> ) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 17, 0x7ffc4c23d33c, 0x7fc0a59a9eb0) = 0
<... hsa_iterate_agents resumed> ) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0, 0x7ffc4c23d380, 0x55a625fbddb8) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa000, 0x55a625fbdbd0, 0x363039) = 0
libamdhip64.so.6->hsa_agent_iterate_isas(0x55a625f5b690, 0x7fc0a441b240, 0x7ffc4c23d2d0, 0x55a625f5b690) = 0
libamdhip64.so.6->hsa_isa_get_info_alt(0x55a625f7bc78, 0, 0x7ffc4c23d2c0, 0x55a625f5b690) = 0
libamdhip64.so.6->hsa_isa_get_info_alt(0x55a625f7bc78, 1, 0x55a625fbddf0, 0) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 4, 0x55a625fbdbe0, 0) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa010, 0x7ffc4c23d2c4, 0x55a625f5b690) = 0
libamdhip64.so.6->hsa_amd_agent_memory_pool_get_info(0x55a625f5b690, 0x55a625f596e0, 1, 0x7ffc4c23d23c) = 0
libamdhip64.so.6->hsa_amd_agent_memory_pool_get_info(0x55a625f5b690, 0x55a625f596e0, 2, 0x55a625fbde70) = 0
libamdhip64.so.6->hsa_amd_agent_memory_pool_get_info(0x55a625f5b690, 0x55a625f596e0, 1, 0x7ffc4c23d1b4) = 0
libamdhip64.so.6->hsa_amd_agent_memory_pool_get_info(0x55a625f5b690, 0x55a625f596e0, 2, 0x55a625fbde70) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa00e, 0x7ffc4c23d2e0, 0x55a625fbd) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa006, 0x7ffc4c23d2c8, 0) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa00f, 0x7ffc4c23d2cc, 0x55a625f5b690) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa009, 0x7ffc4c23d190, 22) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa011, 0x7ffc4c23d170, 14) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa014, 0x55a625fbd55c, 0x55a62601c) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa002, 0x55a625fbd560, 0x55a625fbdea0) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa001, 0x55a625fbd67c, 0x55a625fbdea0) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 18, 0x7ffc4c23cf90, 64) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa003, 0x55a625fbd5d0, 0x7fc0a3e6c688) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa008, 0x55a625fbd5d4, 0x55a625f5b690) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa016, 0x7ffc4c23cf68, 0x55a625f5b690) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa007, 0x55a625fbd8c8, 0x55a625f5b690) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa004, 0x55a625fbda68, 0x55a625f5b690) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa10a, 0x55a625fbda78, 0x55a625f5b690) = 0
libamdhip64.so.6->hsa_amd_agent_memory_pool_get_info(0x55a625f5b690, 0x55a625f596e0, 1, 0x7ffc4c23cefc) = 0
libamdhip64.so.6->hsa_amd_agent_memory_pool_get_info(0x55a625f5b690, 0x55a625f596e0, 2, 0x55a62601bad0) = 0
libamdhip64.so.6->hsa_amd_agent_iterate_memory_pools(0x55a625f5b690, 0x7fc0a441b540, 0x55a625fbd500, 0x55a62601b <unfinished ...>
libamdhip64.so.6->hsa_amd_memory_pool_get_info(0x55a625f822b0, 0, 0x7ffc4c23ce9c, 0x55a625fbd500) = 0
libamdhip64.so.6->hsa_amd_memory_pool_get_info(0x55a625f822b0, 1, 0x7ffc4c23cea0, 0x7ffc4c23ce9c) = 0
libamdhip64.so.6->hsa_amd_agent_memory_pool_get_info(0x55a625f40bd0, 0x55a625f822b0, 0, 0x7ffc4c23cea4) = 0
libamdhip64.so.6->hsa_amd_memory_pool_get_info(0x55a625f822b0, 6, 0x55a625fbda60, 0) = 0
libamdhip64.so.6->hsa_amd_memory_pool_get_info(0x55a625f82640, 0, 0x7ffc4c23ce9c, 0x55a625fbda60) = 0
libamdhip64.so.6->hsa_amd_memory_pool_get_info(0x55a625f82640, 1, 0x7ffc4c23cea0, 0x7ffc4c23ce9c) = 0
libamdhip64.so.6->hsa_amd_memory_pool_get_info(0x55a625f82de0, 0, 0x7ffc4c23ce9c, 0x7ffc4c23cea0) = 0
<... hsa_amd_agent_iterate_memory_pools resumed> ) = 0
libamdhip64.so.6->hsa_amd_memory_pool_get_info(0x55a625f82de0, 2, 0x7ffc4c23cf78, 0x55a62601b3c0) = 0
libamdhip64.so.6->hsa_amd_memory_copy_engine_status(0x55a625f40bd0, 0x55a625f5b690, 0x55a625fbdcb0, 0x7ffc4c23cf78) = 0
libamdhip64.so.6->hsa_amd_memory_copy_engine_status(0x55a625f5b690, 0x55a625f40bd0, 0x55a625fbdcb4, 0) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa114, 0x7ffc4c23d168, 0) = 0
libamdhip64.so.6->hsa_amd_memory_pool_get_info(0x55a625f822b0, 2, 0x7ffc4c23cf80, 0x55a625f5b690) = 0
libamdhip64.so.6->hsa_amd_memory_pool_get_info(0x55a625f822b0, 6, 0x55a625fbdc38, 100) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 8, 0x7ffc4c23cf5c, 0x7fc0a3b1b8f7) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 7, 0x7ffc4c23cf88, 0x55a625f5b690) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 21, 0x7ffc4c23cf58, 0x55a625f5b690) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 22, 0x7ffc4c23cf5a, 0x55a625f5b690) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 20, 0x7ffc4c23d1d0, 0x55a37c63ddcb) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0x300b, 0x55a625fbd650, 0x7fc0a39ff500) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0x3009, 0x55a625fbd5ec, 0x55a625f5b690) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0x300a, 0x55a625fbd5f4, 0x55a625f5b690) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0x3003, 0x7ffc4c23cfc0, 0x55a625f5b690 <unfinished ...>
libhsa-runtime64.so.1->hsa_amd_image_get_info_max_dim(0x55a625f5b690, 0x3003, 0x7ffc4c23cfc0, 0x55a625f5b690) = 0
libhsa-runtime64.so.1->hsa_amd_agent_iterate_memory_pools(0x55a625f40bd0, 0x7fc0a37333c0, 0x55a62601c6c0, 0) = 1
libhsa-runtime64.so.1->hsaKmtGetTileConfig(1, 0x7ffc4c23cbc0, 0, 0x55a625f5b690) = 0
<... hsa_agent_get_info resumed> ) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0x3007, 0x7ffc4c23cfc0, 0x7ffc4c23ce84 <unfinished ...>
libhsa-runtime64.so.1->hsa_amd_image_get_info_max_dim(0x55a625f5b690, 0x3007, 0x7ffc4c23cfc0, 0x55a625f5b690) = 0
<... hsa_agent_get_info resumed> ) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0x3008, 0x7ffc4c23cf60, 0 <unfinished ...>
libhsa-runtime64.so.1->hsa_amd_image_get_info_max_dim(0x55a625f5b690, 0x3008, 0x7ffc4c23cf60, 0x55a625f5b690) = 0
<... hsa_agent_get_info resumed> ) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0x3001, 0x7ffc4c23cf64, 0x7ffc4c23ce84 <unfinished ...>
libhsa-runtime64.so.1->hsa_amd_image_get_info_max_dim(0x55a625f5b690, 0x3001, 0x7ffc4c23cf64, 0x55a625f5b690) = 0
<... hsa_agent_get_info resumed> ) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0x3004, 0x7ffc4c23cfa0, 0x7ffc4c23ce84 <unfinished ...>
libhsa-runtime64.so.1->hsa_amd_image_get_info_max_dim(0x55a625f5b690, 0x3004, 0x7ffc4c23cfa0, 0x55a625f5b690) = 0
<... hsa_agent_get_info resumed> ) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0x3000, 0x7ffc4c23cf80, 0x7ffc4c23ce84 <unfinished ...>
libhsa-runtime64.so.1->hsa_amd_image_get_info_max_dim(0x55a625f5b690, 0x3000, 0x7ffc4c23cf80, 0x55a625f5b690) = 0
<... hsa_agent_get_info resumed> ) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0x3002, 0x7ffc4c23cfc0, 0x7ffc4c23ce84 <unfinished ...>
libhsa-runtime64.so.1->hsa_amd_image_get_info_max_dim(0x55a625f5b690, 0x3002, 0x7ffc4c23cfc0, 0x55a625f5b690) = 0
<... hsa_agent_get_info resumed> ) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 6, 0x55a625fbd8b8, 0x7fc0a59a9e80) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa007, 0x55a625fbd5dc, 0x55a625f5b690) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa00b, 0x55a625fbd8a8, 0x55a625f5b690) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa00a, 0x7ffc4c23cf64, 0x55a625f5b690) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 18, 0x7ffc4c23cfc0, 0x55a625f5b690) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa012, 0x7ffc4c23cf80, 0x55a625f5b690) = 0
libamdhip64.so.6->hsa_system_get_info(513, 0x55a625fbda34, 0x55a625f40010, 0x55a37c63dcfb) = 0
libamdhip64.so.6->hsa_system_get_info(514, 0x55a625fbda38, 0, 1) = 0
libamdhip64.so.6->hsa_agent_get_info(0x55a625f5b690, 0xa013, 0x55a625fbda3c, 0) = 0
libamdhip64.so.6->hsa_system_get_info(517, 0x55a625fbda5a, 0, 0) = 0
libamdhip64.so.6->hsa_amd_memory_pool_allocate(0x55a625f5a880, 0x100000, 0, 0x7ffc4c23d1c0 <unfinished ...>
libhsa-runtime64.so.1->hsaKmtAllocMemory(0, 0x100000, 8256, 0x7ffc4c23d060 <unfinished ...>
libhsakmt.so.1->hsaKmtAllocMemoryAlign(0, 0x100000, 0, 8256) = 0
<... hsaKmtAllocMemory resumed> ) = 0
<... hsa_amd_memory_pool_allocate resumed> ) = 0
libamdhip64.so.6->hsa_amd_agents_allow_access(1, 0x55a625fbd330, 0, 0x7fbfa0200000 <unfinished ...>
libhsa-runtime64.so.1->hsaKmtQueryPointerInfo(0x7fbfa0200000, 0x7ffc4c23cfb0, 1, 3) = 0
libhsa-runtime64.so.1->hsaKmtMapMemoryToGPUNodes(0x7fbfa0200000, 0x100000, 0x7ffc4c23d088, 0) = 0
<... hsa_amd_agents_allow_access resumed> ) = 0
libamdhip64.so.6->hsa_signal_create(1, 0, 0, 0x55a625fbdc20 <unfinished ...>
libhsa-runtime64.so.1->hsaKmtCreateEvent(0x7ffc4c23d190, 0, 0, 0x7ffc4c23d188) = 0
<... hsa_signal_create resumed> ) = 0
libamdhip64.so.6->hsa_amd_memory_pool_allocate(0x55a625f5a880, 0x400000, 0, 0x7ffc4c23d230 <unfinished ...>
libhsa-runtime64.so.1->hsaKmtAllocMemory(0, 0x400000, 8256, 0x7ffc4c23d0d0 <unfinished ...>
libhsakmt.so.1->hsaKmtAllocMemoryAlign(0, 0x400000, 0, 8256) = 0
<... hsaKmtAllocMemory resumed> ) = 0
<... hsa_amd_memory_pool_allocate resumed> ) = 0
libamdhip64.so.6->hsa_amd_agents_allow_access(1, 0x55a625fbd330, 0, 0x7fbf8f800000 <unfinished ...>
libhsa-runtime64.so.1->hsaKmtQueryPointerInfo(0x7fbf8f800000, 0x7ffc4c23d020, 1, 3) = 0
libhsa-runtime64.so.1->hsaKmtMapMemoryToGPUNodes(0x7fbf8f800000, 0x400000, 0x7ffc4c23d0f8, 0) = 0
<... hsa_amd_agents_allow_access resumed> ) = 0
libamdhip64.so.6->hsa_amd_memory_pool_allocate(0x55a625f596e0, 56, 0, 0x7ffc4c23d1b0 <unfinished ...>
libhsa-runtime64.so.1->hsaKmtAllocMemory(0, 4096, 64, 0x7ffc4c23d050 <unfinished ...>
libhsakmt.so.1->hsaKmtAllocMemoryAlign(0, 4096, 0, 64) = 0
<... hsaKmtAllocMemory resumed> ) = 0
<... hsa_amd_memory_pool_allocate resumed> ) = 0
libamdhip64.so.6->hsa_amd_agents_allow_access(1, 0x55a625fbd330, 0, 0x7fc0a3f34000 <unfinished ...>
libhsa-runtime64.so.1->hsaKmtQueryPointerInfo(0x7fc0a3f34000, 0x7ffc4c23cfa0, 1, 3) = 0
libhsa-runtime64.so.1->hsaKmtMapMemoryToGPUNodes(0x7fc0a3f34000, 4096, 0x7ffc4c23d078, 0) = 0
<... hsa_amd_agents_allow_access resumed> ) = 0
libamdhip64.so.6->hsa_amd_memory_pool_allocate(0x55a625f822b0, 1, 0, 0x7ffc4c23d5e0 <unfinished ...>
libhsa-runtime64.so.1->hsaKmtAllocMemory(1, 0x200000, 8321, 0x7ffc4c23d330 <unfinished ...>
libhsakmt.so.1->hsaKmtAllocMemoryAlign(1, 0x200000, 0, 8321) = 0
<... hsaKmtAllocMemory resumed> ) = 0
libhsa-runtime64.so.1->hsaKmtMapMemoryToGPUNodes(0x7fbf8f400000, 0x200000, 0x7ffc4c23d330, 0) = 0
<... hsa_amd_memory_pool_allocate resumed> ) = 0
<... hipMalloc resumed> ) = 0
libamdhip64.so.6->hsa_amd_memory_pool_free(0x7fbf8f800000, 0x7fbf8f800000, 0x400000, 16 <unfinished ...>
libhsa-runtime64.so.1->hsaKmtUnmapMemoryToGPU(0x7fbf8f800000, 0x7fbf8f800000, 0x400000, 0) = 0
libhsa-runtime64.so.1->hsaKmtFreeMemory(0x7fbf8f800000, 0x400000, 0, 0x7fc0a3bf1ad0) = 0
<... hsa_amd_memory_pool_free resumed> ) = 0
libamdhip64.so.6->hsa_amd_memory_pool_free(0x7fc0a3f34000, 0x7fc0a3f34000, 56, 3072 <unfinished ...>
libhsa-runtime64.so.1->hsaKmtUnmapMemoryToGPU(0x7fc0a3f34000, 0x7fc0a3f34000, 4096, 0) = 0
libhsa-runtime64.so.1->hsaKmtFreeMemory(0x7fc0a3f34000, 4096, 0, 0x7fc0a3bf1ad0) = 0
<... hsa_amd_memory_pool_free resumed> ) = 0
libamdhip64.so.6->hsa_amd_memory_pool_free(0x7fbfa0200000, 0x7fbfa0200000, 0x100000, 0x55a37c60e1a7 <unfinished ...>
libhsa-runtime64.so.1->hsaKmtUnmapMemoryToGPU(0x7fbfa0200000, 0x7fbfa0200000, 0x100000, 0) = 0
libhsa-runtime64.so.1->hsaKmtFreeMemory(0x7fbfa0200000, 0x100000, 0, 0x7fc0a3bf1ad0) = 0
<... hsa_amd_memory_pool_free resumed> ) = 0
libamdhip64.so.6->hsa_signal_destroy(0x7fc0a33ffe00, 0x55a62601b, 0x55a6260272e0, 0x7fc0a3bf1ad0) = 0
libamdhip64.so.6->hsa_shut_down(0x55a626026, 0x55a626026, 0x55a626026fe0, 0x7fc0a3bf1ad0 <unfinished ...>
libhsa-runtime64.so.1->hsaKmtFreeMemory(0x7fbfa2800000, 0x100000000, 0x55a625f40010, 0x55a37c63fab4) = 0
libhsa-runtime64.so.1->hsaKmtUnmapMemoryToGPU(0x7fc0a5bb2000, 0x7fc0a5bb2000, 4096, 0) = 0
libhsa-runtime64.so.1->hsaKmtFreeMemory(0x7fc0a5bb2000, 4096, 0, 0x55a37c639cbd) = 0
libhsa-runtime64.so.1->hsaKmtSetEvent(0x55a625f855a0, 1, 0x71fcca6a3d5d5276, 0x55a625f5bd70) = 0
libhsa-runtime64.so.1->hsaKmtDestroyEvent(0x55a625f84e90, 0x55a625f84, 0x55a625f85190, 0x7fc0a3bf1ae8) = 0
libhsa-runtime64.so.1->hsaKmtDestroyEvent(0x55a625f85900, 0x55a625f85, 0x55a625f84fc0, 0x7fc0a3bf1ae8) = 0
libhsa-runtime64.so.1->hsaKmtUnmapMemoryToGPU(0x7fc0a3200000, 0x7fc0a3200000, 0x200000, 0) = 0
libhsa-runtime64.so.1->hsaKmtFreeMemory(0x7fc0a3200000, 0x200000, 0, 0x7fc0a3bf1ad0) = 0
libhsa-runtime64.so.1->hsaKmtDestroyEvent(0x55a6260274f0, 0, 0, 0x55a37f998f05) = 0
libhsa-runtime64.so.1->hsaKmtDestroyEvent(0x55a625f855a0, 0x55a626027, 0, 0x7fc0a3bf1ae0) = 0
libhsa-runtime64.so.1->hsaKmtRuntimeDisable(0x55a625f545f0, 0x7fc0a3bf1d20, 529, 33 <unfinished ...>
libhsakmt.so.1->hsaKmtCheckRuntimeDebugSupport(0x55a625f545f0, 0x7fc0a3bf1d20, 529, 33 <unfinished ...>
libhsakmt.so.1->hsaKmtAcquireSystemProperties(0x7ffc4c23da60, 0x7fc0a3bf1d20, 529, 0) = 0
libhsakmt.so.1->hsaKmtGetNodeProperties(0, 0x7ffc4c23da70, 2, 0) = 0
libhsakmt.so.1->hsaKmtGetNodeProperties(1, 0x7ffc4c23da70, 0, 0) = 0
libhsakmt.so.1->hsaKmtGetVersion(0x7ffc4c23da58, 0, 0, 0x7fc0a5bb4fff) = 0
<... hsaKmtCheckRuntimeDebugSupport resumed> ) = 0
<... hsaKmtRuntimeDisable resumed> ) = 0
libhsa-runtime64.so.1->hsaKmtReleaseSystemProperties(3, 0xc0104b25, 0, 0x7fc0a3b168db) = 0
libhsa-runtime64.so.1->hsaKmtCloseKFD(0x7fc0a5a49120, 0, 0, 0x7fc0a3bf1ad0) = 0
<... hsa_shut_down resumed> ) = 0
+++ exited (status 0) +++
Reply to: