search

CHIP-SPV / chipStar

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

RISC-V OpenCL runtime failure `InvalidBuiltinSetName` #922

Open pvelesko opened 2 months ago

pvelesko commented 2 months ago 
InvalidBuiltinSetName: Expects OpenCL.std. Actual is OpenCL.DebugInfo.100 [Src: /home/clement/sft-riscvpi-freedom-u-sdk/soft_3rdpart/IMG_GPU/linux/llvm/llvm.src/spv-translator/lib/SPIRV/libSPIRV/SPIRVModule.cpp:776 SPIRVBuiltinSetNameMap::rfind(BuiltinSetName, &BuiltinSet) ]
Aborted
pvelesko@macaroni:~/chipStar/build$ ./samples/0_MatrixMultiply/MatrixMultiply
CHIP info [TID 63546] [1726492636.292818378] : CHIP_PLATFORM=0
CHIP info [TID 63546] [1726492636.294501906] : CHIP_DEVICE_TYPE=default
CHIP info [TID 63546] [1726492636.294621158] : CHIP_DEVICE=0
CHIP info [TID 63546] [1726492636.294741160] : CHIP_BE=opencl
CHIP info [TID 63546] [1726492636.294839161] : CHIP_DUMP_SPIRV=off
CHIP info [TID 63546] [1726492636.294952663] : CHIP_JIT_FLAGS_OVERRIDE=-cl-kernel-arg-info -cl-std=CL3.0
CHIP info [TID 63546] [1726492636.295051415] : CHIP_L0_COLLECT_EVENTS_TIMEOUT=0
CHIP info [TID 63546] [1726492636.295177667] : CHIP_L0_EVENT_TIMEOUT=0
CHIP info [TID 63546] [1726492636.295281419] : CHIP_SKIP_UNINIT=off
CHIP debug [TID 63546] [1726492636.300568256] : __hipRegisterFatBinary
CHIP debug [TID 63546] [1726492636.300722009] : CHIPDriver Initialize
CHIP debug [TID 63546] [1726492636.300819261] : CHIPBE=OPENCL... Initializing OpenCL Backend
CHIP debug [TID 63546] [1726492636.301050014] : Backend Base Constructor
CHIP debug [TID 63546] [1726492636.362827038] : CHIP_PLATFORM=0 Selected OpenCL platform PowerVR
CHIP info [TID 63546] [1726492636.363379297] : OpenCL Devices of type default with SPIR-V_1 support:
PowerVR B-Series BXE-4-32  is supported.

CHIP debug [TID 63546] [1726492636.363524800] : CHIP_DEVICE=0 Selected OpenCL device PowerVR B-Series BXE-4-32
CHIP debug [TID 63546] [1726492636.365165577] : cl_ext_float_atomics extension is not supported
CHIP debug [TID 63546] [1726492636.365433581] : cl_ext_float_atomics extension is not supported
CHIP debug [TID 63546] [1726492636.365965340] : Chosen allocation strategy: coarse-grain SVM.
CHIP warning [TID 63546] [1726492636.366287346] : The device might not support subgroup size 32, warp-size sensitive kernels might not work correctly.
CHIP debug [TID 63546] [1726492636.369178893] : Queue() 0x2ab8b17700
CHIP debug [TID 63546] [1726492636.369687152] : Bundle entry ID 0 is: 'host-x86_64-unknown-linux--'

CHIP debug [TID 63546] [1726492636.369804154] : Not a SPIR-V triple, ignoring

CHIP debug [TID 63546] [1726492636.369910656] : Bundle entry ID 1 is: 'hip-spirv64----generic'

CHIP debug [TID 63546] [1726492636.370175410] : Registered SPIR-V module 0x2ab8b18380, source-binary=0x2ab8ae2000
CHIP debug [TID 63546] [1726492636.370312412] : chipstar::Module 0x2ab8b18380: register function (0x2ab8ae5db8) _Z12gpuMatrixMulPKfS0_Pfjjj
CHIP debug [TID 63546] [1726492636.370614667] : chipstar::Module 0x2ab8b18380: Register variable (0x2ab8ae61e8) size=4, name=__chipspv_abort_called
CHIP debug [TID 63546] [1726492636.371396680] : Device->copy_device_properties()
Device name PowerVR B-Series BXE-4-32

CHIP debug [TID 63546] [1726492647.154393448] : Currently used memory on dev PowerVR B-Series BXE-4-32: 4 M

CHIP debug [TID 63546] [1726492647.157374997] : chipstar::AllocationTracker::recordAllocation size: 4194304 HOST 0x0 DEV 0x3f8422f000 TYPE 2
CHIP debug [TID 63546] [1726492647.157458249] : hipMallocInternal(ptr=0x3f8422f000, size=4194304)
CHIP debug [TID 63546] [1726492647.157516500] : Currently used memory on dev PowerVR B-Series BXE-4-32: 8 M

CHIP debug [TID 63546] [1726492647.160197794] : chipstar::AllocationTracker::recordAllocation size: 4194304 HOST 0x0 DEV 0x3f83e2f000 TYPE 2
CHIP debug [TID 63546] [1726492647.160254795] : hipMallocInternal(ptr=0x3f83e2f000, size=4194304)
CHIP debug [TID 63546] [1726492647.160307296] : Currently used memory on dev PowerVR B-Series BXE-4-32: 12 M

CHIP debug [TID 63546] [1726492647.162896589] : chipstar::AllocationTracker::recordAllocation size: 4194304 HOST 0x0 DEV 0x3f83a2f000 TYPE 2
CHIP debug [TID 63546] [1726492647.162949840] : hipMallocInternal(ptr=0x3f83a2f000, size=4194304)
CHIP debug [TID 63546] [1726492647.163041841] : hipMemcpy Dst=0x3f8422f000 Src=0x3f85232010 Size=4194304 Kind=hipMemcpyHostToDevice
CHIP debug [TID 63546] [1726492647.163444848] : Setting LastEvent for 0x2ab8b17700 0x0 -> 0x2ab8b08730
CHIP debug [TID 63546] [1726492647.173152759] : hipMemcpy Dst=0x3f83e2f000 Src=0x3f84e31010 Size=4194304 Kind=hipMemcpyHostToDevice
CHIP debug [TID 63546] [1726492647.173384263] : Setting LastEvent for 0x2ab8b17700 0x0 -> 0x2ab8b08730
CHIP debug [TID 63546] [1726492647.186591982] : Queue 0x2ab8b17700: switching mode to profiling
CHIP debug [TID 63546] [1726492647.187595248] : Setting LastEvent for 0x2ab8b17700 0x0 -> 0x2ab8b08730
CHIP debug [TID 63546] [1726492647.188305760] : Setting LastEvent for 0x2ab8b17700 0x2ab8b08730 -> 0x2ab8b1bc40
CHIP debug [TID 63546] [1726492647.188864020] : __hipPushCallConfiguration()
CHIP debug [TID 63546] [1726492647.189281026] : __hipPopCallConfiguration()
CHIP debug [TID 63546] [1726492647.189698033] : Finalize module 0x2ab8b18380
CHIP debug [TID 63546] [1726492647.204651281] : Compile module 0x2ab8b18380
InvalidBuiltinSetName: Expects OpenCL.std. Actual is OpenCL.DebugInfo.100 [Src: /home/clement/sft-riscvpi-freedom-u-sdk/soft_3rdpart/IMG_GPU/linux/llvm/llvm.src/spv-translator/lib/SPIRV/libSPIRV/SPIRVModule.cpp:776 SPIRVBuiltinSetNameMap::rfind(BuiltinSetName, &BuiltinSet) ]
Aborted