GPU code throwing exception at runtime

[Shukla__Gagandeep]

Hi,

I am working on some code using OneAPI (Latest Compiler beta07) and the code is throwing exeption at runtime in windows. I am using Visual Studio 2017 to build the code.

At compile time, I get the following warning:

2>a-0ca30d.obj : : warning LNK4078: multiple '__CLANG_OFFLOAD_BUNDLE_SIZE__syc' sections found with different attributes (40100040)
2>a-0ca30d.obj : : warning LNK4078: multiple '__CLANG_OFFLOAD_BUNDLE__sycl-spi' sections found with different attributes (40500040)

At run-time, I get following exception:

my device: Intel(R) HD Graphics 520
Native API failed. Native API returns: -46 (CL_INVALID_KERNEL_NAME) -46 (CL_INVALID_KERNEL_NAME)
0x00007FF92330A799 (0x0000002EEFAF8A80 0x0000000000000000 0x0000002EEFAF9EA8 0x00007FF64CB058A8), RaiseException() + 0x69 bytes(s)
0x00007FF64CBB12CD (0x00007FF64CAE0000 0x0000002EEFAFA7F0 0x0000002EEFAF9880 0x0000002EEFAFB040), _CxxThrowException() + 0xAD bytes(s), d:\agent\_work\2\s\src\vctools\crt\vcruntime\src\eh\throw.cpp, line 133
0x00007FF64CB5813F (0x00007FF64CB580D0 0x0000002EEFAFEE80 0x0000002EEFAFEE80 0x0000000000000004), syclMatchMulti() + 0xBBF bytes(s), C:\Users\intel\source\repos\regParser_oneapi\regParserLib\Match_SYCL.cpp, line 262 + 0x28 byte(s)
0x00007FF64CBBFF70 (0x00007FF64CB580D0 0x0000002EEFAF9EA8 0x0000002E00000100 0x00007FF8D27AA832), _CallSettingFrame() + 0x20 bytes(s), d:\agent\_work\2\s\src\vctools\crt\vcruntime\src\eh\amd64\handlers.asm, line 50
0x00007FF64CBB50E4 (0x0000016400000000 0x0000002EEFAFB040 0x0000000000000000 0x0000000000000000), __FrameHandler3::CxxCallCatchBlock() + 0xE8 bytes(s), d:\agent\_work\2\s\src\vctools\crt\vcruntime\src\eh\frame.cpp, line 1528 + 0x13 byte(s)
0x00007FF925FE0616 (0x0000002EEFAFF1A8 0x00007FF64CB02333 0x0000002EEFAFF170 0x0000002EEFAFF170), RtlCaptureContext() + 0x566 bytes(s)
0x00007FF64CB57B60 (0x0000002EEFAFF858 0x0000002EEFAFF658 0x00000164BA970420 0x00007FF64CB10C64), syclMatchMulti() + 0x5E0 bytes(s), C:\Users\intel\source\repos\regParser_oneapi\regParserLib\Match_SYCL.cpp, line 186 + 0xC7 byte(s)
0x00007FF64CAF4769 (0x0000000000000000 0x00000164B58D8110 0x00000164B58DCE10 0x00007FF64CB12628), sycl_match_multi() + 0x129 bytes(s), C:\Users\intel\source\repos\regParser_oneapi\regParser_oneapi\regParser_oneapi.cpp, line 438 + 0x38 byte(s)
0x00007FF64CAF4E31 (0x0000000000000000 0x0000000000000000 0x0000000000000000 0x0000000000000000), main() + 0x3F1 bytes(s), C:\Users\intel\source\repos\regParser_oneapi\regParser_oneapi\regParser_oneapi.cpp, line 501 + 0x43 byte(s)
0x00007FF64CB792A0 (0x0000000000000000 0x0000000000000000 0x0000000000000000 0x0000000000000000), __scrt_common_main_seh() + 0x10C bytes(s), d:\agent\_work\2\s\src\vctools\crt\vcstartup\src\startup\exe_common.inl, line 288 + 0x22 byte(s)
0x00007FF924C27BD4 (0x0000000000000000 0x0000000000000000 0x0000000000000000 0x0000000000000000), BaseThreadInitThunk() + 0x14 bytes(s)
0x00007FF925FACE51 (0x0000000000000000 0x0000000000000000 0x0000000000000000 0x0000000000000000), RtlUserThreadStart() + 0x21 bytes(s)

C:\Users\intel\source\repos\regParser_oneapi\x64\Debug\regParser_oneapi.exe (process 15420) exited with code -529697949.

If I don't catch and rethrow exception, I get:

my device: Intel(R) HD Graphics 520
0x00007FF92330A799 (0x000000DF134FB0E0 0x000000000000000F 0x000002CAD9491570 0x000000DF134FD9B0), RaiseException() + 0x69 bytes(s)
0x00007FF8FA119097 (0xFFFFFFFFFFFFFFFE 0x000000DF134FD010 0x000002CAD906E870 0x000002CAD906DF40), ?do_encoding@?$codecvt@_SDU_Mbstatet@@@std@@MEBAHXZ() + 0x2E7 bytes(s)
0x00007FF8FA1192C1 (0x000002CAD906E870 0x000002CAD906DF40 0xFFFFFFFFFFFFFFFE 0xFFFFFFFFFFFFFFFF), ?__ExceptionPtrRethrow@@YAXPEBX@Z() + 0x11 bytes(s)
0x00007FF8D278B219 (0x000000DF134FB290 0x00007FF8FA129001 0x000000DF134FD010 0x000002CAD906E870), __sycl_unregister_lib() + 0x3199 bytes(s)
0x00007FF8D278AEEB (0x000072BDA1E18919 0x000000DF134FC140 0x000000DF134FB3C0 0x00007FF915304BE6), __sycl_unregister_lib() + 0x2E6B bytes(s)
0x00007FF8D2781D04 (0x00007FF8D2781C70 0x000000DF134FDA80 0x000000DF134FDA80 0x000000DF134FBDE8), ?prefetch_usm@MemoryManager@detail@sycl@cl@@SAXPEAXV?$shared_ptr@Vqueue_impl@detail@sycl@cl@@@std@@_KV?$vector@PEAU_pi_event@@V?$allocator@PEAU_pi_event@@@std@@@6@AEAPEAU_pi_event@@@Z() + 0x24474 bytes(s)
0x00007FF915301030 (0x00007FF8D2781C70 0x000000DF134FC6C8 0x000000DF00000100 0x0000000000000000)
0x00007FF9153032E8 (0x000000FC00000000 0x000000DF134FD860 0x0000000000000000 0x0000000000000000), _is_exception_typeof() + 0x1018 bytes(s)
0x00007FF925FE0616 (0x0000000000003501 0x000002CA000003FF 0x000000DF134FE801 0x000002CAD9538F50), RtlCaptureContext() + 0x566 bytes(s)
0x00007FF8D278171F (0x000002CAD4C602A8 0x00007FF925F84C9B 0x0000000000000020 0x000002CAD4C60CC0), ?prefetch_usm@MemoryManager@detail@sycl@cl@@SAXPEAXV?$shared_ptr@Vqueue_impl@detail@sycl@cl@@@std@@_KV?$vector@PEAU_pi_event@@V?$allocator@PEAU_pi_event@@@std@@@6@AEAPEAU_pi_event@@@Z() + 0x23E8F bytes(s)
0x00007FF8D27A3D02 (0x000000DF134FE400 0x00007FF63022CB6F 0x000000DF134FE801 0x000002CAD906BAF0), ?flush@stream_impl@detail@sycl@cl@@QEAAXXZ() + 0x114C2 bytes(s)
0x00007FF8D279705C (0x000002CAD95EE3F0 0x00007FF8D27E56FF 0x0000000000000050 0x000002CAD906CCF0), ?flush@stream_impl@detail@sycl@cl@@QEAAXXZ() + 0x481C bytes(s)
0x00007FF8D27AAA35 (0x000000DF134FE8E8 0x00007FF63022C1C6 0x0000000000000000 0x000000DF134FE6B0), ?flush@stream_impl@detail@sycl@cl@@QEAAXXZ() + 0x181F5 bytes(s)
0x00007FF8D27CBE85 (0x000002CAD9CE72C0 0x00007F000020312E 0x000000000000000C 0x00007FF925F7C43F), ?finalize@handler@sycl@cl@@AEAA?AVevent@23@XZ() + 0x10B5 bytes(s)
0x00007FF8D27D6886 (0x000000DF134FED98 0x00007FF630228863 0x000000003A5CADC8 0x000000DF134FED40), ??$get_property@Venable_profiling@queue@property@sycl@cl@@@ordered_queue@sycl@cl@@QEBA?AVenable_profiling@queue@property@12@XZ() + 0x2F6 bytes(s)
0x00007FF8D27D60E6 (0x000000DF134FEEB0 0x0000000000000000 0x00007FF63034F25C 0x00007FF63024E06A), ?submit_impl@queue@sycl@cl@@AEAA?AVevent@23@V?$function@$$A6AXAEAVhandler@sycl@cl@@@Z@std@@AEBUcode_location@detail@23@@Z() + 0x56 bytes(s)
0x00007FF6302281DE (0x000000DF134FF128 0x00007FF6301D2453 0x00007FF63034D630 0x000000DF134FEEA8), cl::sycl::queue::submit<`lambda at Match_SYCL.cpp:186:28'>() + 0x9E bytes(s), C:\PROGRA~2\INTELO~1\compiler\2021~4.1-B\windows\include\sycl\CL\sycl\queue.hpp, line 185 + 0x6B byte(s)
0x00007FF630227B50 (0x000000DF134FF7D8 0x000000DF134FF5D8 0x000002CAD9CFCBD0 0x00007FF6301E0C64), syclMatchMulti() + 0x5D0 bytes(s), C:\Users\intel\source\repos\regParser_oneapi\regParserLib\Match_SYCL.cpp, line 186 + 0xBB byte(s)
0x00007FF6301C4769 (0x0000000000000000 0x000002CAD4D3E610 0x000002CAD4D3D500 0x00007FF6301E2628), sycl_match_multi() + 0x129 bytes(s), C:\Users\intel\source\repos\regParser_oneapi\regParser_oneapi\regParser_oneapi.cpp, line 438 + 0x38 byte(s)
0x00007FF6301C4E31 (0x0000000000000000 0x0000000000000000 0x0000000000000000 0x0000000000000000), main() + 0x3F1 bytes(s), C:\Users\intel\source\repos\regParser_oneapi\regParser_oneapi\regParser_oneapi.cpp, line 501 + 0x43 byte(s)
0x00007FF630249200 (0x0000000000000000 0x0000000000000000 0x0000000000000000 0x0000000000000000), __scrt_common_main_seh() + 0x10C bytes(s), d:\agent\_work\2\s\src\vctools\crt\vcstartup\src\startup\exe_common.inl, line 288 + 0x22 byte(s)
0x00007FF924C27BD4 (0x0000000000000000 0x0000000000000000 0x0000000000000000 0x0000000000000000), BaseThreadInitThunk() + 0x14 bytes(s)
0x00007FF925FACE51 (0x0000000000000000 0x0000000000000000 0x0000000000000000 0x0000000000000000), RtlUserThreadStart() + 0x21 bytes(s)

C:\Users\intel\source\repos\regParser_oneapi\x64\Debug\regParser_oneapi.exe (process 22468) exited with code -529697949.

Regards,
Gagan

[RahulV_intel]

Hi Gagan,

Do you mind sharing your minimal reproducible source code that is causing the error?

Thanks,

Rahul

[RahulV_intel]

Hi @Shukla__Gagandeep ,

Just a quick reminder to share the source code that is causing error.

Thanks,

Rahul

[RahulV_intel]

Hi,

I have not heard back from you. So, I will go ahead and close this thread. Feel free to post a new question if you still have any issues.

--Rahul

[Sergey_S_Intel2]

I see particular the same things with beta8
PLEASE submit a bug report to https://software.intel.com/en-us/support/priority-support and include the crash backtrace.
0x00007FFDC30C9159 (0x000000B2373ED6F0 0x000000B2373ED6A0 0x000002368FFE4200 0x000000B2373EE180), RaiseException() + 0x69 bytes(s)
0x00007FFDB059485D (0x00007FFD4C710000 0x000000000000000D 0x000002369265CD20 0x0000000000000013), _CxxThrowException() + 0xAD bytes(s)
0x00007FFD4C85FF94 (0x000000B2373ED880 0x000002369265B600 0x0000000100000503 0x0000000000000000), ?prefetch_usm@MemoryManager@detail@sycl@cl@@SAXPEAXV?$shared_ptr@Vqueue_impl@detail@sycl@cl@@@std@@_KV?$vector@PEAU_pi_event@@V?$allocator@PEAU_pi_event@@@std@@@6@AEAPEAU_pi_event@@@Z() + 0x22E14 bytes(s)
0x00007FFD4C86205B (0x00007FFD4C95C138 0x00007FFDC6719880 0x000000B2373EE9B0 0x000000B2373EE588), ?prefetch_usm@MemoryManager@detail@sycl@cl@@SAXPEAXV?$shared_ptr@Vqueue_impl@detail@sycl@cl@@@std@@_KV?$vector@PEAU_pi_event@@V?$allocator@PEAU_pi_event@@@std@@@6@AEAPEAU_pi_event@@@Z() + 0x24EDB bytes(s)
0x00007FFD4C863583 (0x000002368F7EC108 0x00007FFD6B58899D 0x000002368ECD9138 0x000002368F71B740), ?prefetch_usm@MemoryManager@detail@sycl@cl@@SAXPEAXV?$shared_ptr@Vqueue_impl@detail@sycl@cl@@@std@@_KV?$vector@PEAU_pi_event@@V?$allocator@PEAU_pi_event@@@std@@@6@AEAPEAU_pi_event@@@Z() + 0x26403 bytes(s)
0x00007FFD4C88A9E5 (0x0000000000000040 0xFFFFFFFF00000000 0x00000236929C6001 0x0000000000000000), ?flush@stream_impl@detail@sycl@cl@@QEAAXXZ() + 0x12025 bytes(s)
0x00007FFD4C87CD93 (0x00000000000001A8 0x00007FFD00000000 0x0000000000000000 0x00007FFD33EC9F5F), ?flush@stream_impl@detail@sycl@cl@@QEAAXXZ() + 0x43D3 bytes(s)
0x00007FFD4C894650 (0x000000B2373EEC10 0x0000000000000040 0x0000000000000010 0x0000000000000000), ?flush@stream_impl@detail@sycl@cl@@QEAAXXZ() + 0x1BC90 bytes(s)
0x00007FFD4C8B8E55 (0x0000000200000000 0x00007FFD00000001 0x0000000200000000 0x0000000000000018), ?finalize@handler@sycl@cl@@AEAA?AVevent@23@XZ() + 0x1495 bytes(s)
0x00007FFD4C8C5BB6 (0x000000B2373EEDA0 0x00007FFD30672521 0x00007FFD36C801A0 0x00007FFD4C8B4701), ??$get_property@Venable_profiling@queue@property@sycl@cl@@@queue@sycl@cl@@QEBA?AVenable_profiling@0property@12@XZ() + 0x426 bytes(s)
0x00007FFD4C8C52E6 (0x0000000000000000 0x00007FFD6B8B258A 0xFFFFFFFFFFFFFFFE 0x000002368F7EA6C8), ?submit_impl@queue@sycl@cl@@AEAA?AVevent@23@V?$function@$$A6AXAEAVhandler@sycl@cl@@@Z@std@@AEBUcode_location@detail@23@@Z() + 0x56 bytes(s)
0x00007FFD30671179 (0x000002368F7EA6C8 0x000002368E98F688 0x0000000000000000 0x000000B200000000), ?custom_blas_gemm_c_long@@YAXPEAX00_K11@Z() + 0x179 bytes(s)
0x00007FFD711080BC (0x0000000000000000 0x000002368C8C0000 0x0000023600000000 0x000002368C8C0000), PyInit_backend() + 0x36B6C bytes(s)
0x00007FFD710EEB08 (0x00007FFD6BB7B970 0x0000000000000000 0x0000000000000001 0x0000000000000003), PyInit_backend() + 0x1D5B8 bytes(s)
0x00007FFD6B8B5A05 (0x0000000000000000 0x000000B2373EF268 0x000002368F8791D0 0x00007FFDC66D267D), _PyMethodDef_RawFastCallKeywords() + 0x355 bytes(s)
0x00007FFD6B8B62BA (0x000002368F7DEB30 0x000002368E72E598 0x000002368F7E0408 0x000002368C9C8B20), _PyMethodDef_RawFastCallKeywords() + 0xC0A bytes(s)
0x00007FFD6B8B697F (0x000002368E72E598 0x0000000000000000 0x000002368F7D89C0 0x0000000000000043), _PyEval_EvalFrameDefault() + 0x4AF bytes(s)
0x00007FFD6B8B3BC9 (0x0000000000000003 0x000002368E9907F0 0x000000B2373EF4E8 0x000002368EE6F4D0), _PyEval_EvalCodeWithName() + 0x199 bytes(s)
0x00007FFD6B8B636F (0x0000023600000000 0x000002368E72E598 0x000000B2373EF500 0x000002368C9C8B20), _PyMethodDef_RawFastCallKeywords() + 0xCBF bytes(s)
0x00007FFD6B8B6DC4 (0x000000B2373EF708 0x000002368EE6F2E8 0x000002368E9321F0 0x000000B2373EF708), _PyEval_EvalFrameDefault() + 0x8F4 bytes(s)
0x00007FFD6B8B6256 (0x00007FFD6BBFB220 0x000002368E9929F0 0x00000236920AB778 0x000002368C9C8B20), _PyMethodDef_RawFastCallKeywords() + 0xBA6 bytes(s)
0x00007FFD6B8B697F (0x000002368E72E548 0x0000000000000000 0x000002368E92A810 0x0000000000000040), _PyEval_EvalFrameDefault() + 0x4AF bytes(s)
0x00007FFD6B8B3BC9 (0x0000000000000000 0x000000B2373EF900 0x0000000000000000 0x0000000000000000), _PyEval_EvalCodeWithName() + 0x199 bytes(s)
0x00007FFD6B88D553 (0x000002368E92A810 0x000002368E7A5098 0x0000000000000000 0x0000000000000000), PyEval_EvalCodeEx() + 0x9B bytes(s)
0x00007FFD6B88D4B1 (0x000002368E980990 0x000002368E7A5098 0x000002368E7A5098 0x000002368EADB3C0), PyEval_EvalCode() + 0x2D bytes(s)
0x00007FFD6B88D45B (0x000002368E980990 0x000002368EADB3C0 0x0000000000000101 0x6031D03937083961), PyFuture_FromASTObject() + 0x157 bytes(s)
0x00007FFD6BA25CE5 (0x000000B2373EFB20 0x000002368E7A5098 0x000002368E921490 0x000002368E7A51D8), PyRun_FileExFlags() + 0xC5 bytes(s)
0x00007FFD6BA2650C (0x000002368C9B5A10 0x0000000000000001 0x000000B2373EFB20 0x000000B2373EFB20), PyRun_SimpleFileExFlags() + 0x24C bytes(s)
0x00007FFD6BA25BB3 (0x0000000000000000 0x000002368C9C0060 0x000002368E97B490 0x0000000000000000), PyRun_AnyFileExFlags() + 0x63 bytes(s)
0x00007FFD6B9714F3 (0x000000B2373EFB90 0x000000B2373EFB99 0x0000000000000000 0x0000000000000000), _Py_UnixMain() + 0x573 bytes(s)
0x00007FFD6B97159B (0x000000B2373EFB90 0x0000000000000000 0x0074007900000000 0x0000000000000000), _Py_UnixMain() + 0x61B bytes(s)
0x00007FFD6B903782 (0x000000B200000000 0x000000B2373EFB90 0x0000000000000000 0x000002368C9B5770), PyErr_NoMemory() + 0x25012 bytes(s)
0x00007FFD6B8B8FB1 (0x0000DFA72CD8CB7B 0x0000000000000000 0x0000000000000000 0x00007FFDC379E211), PyBytes_AsString() + 0xCD bytes(s)
0x00007FFD6B8B89FE (0x0000000000000000 0x0000000000000000 0x0000000000000000 0x0000000000000000), Py_Main() + 0x52 bytes(s)
0x00007FF6E5E81268 (0x0000000000000000 0x0000000000000000 0x000000B237119000 0x00007FF6E5E81368)
0x00007FFDC65E7974 (0x0000000000000000 0x0000000000000000 0x0000000000000000 0x0000000000000000), BaseThreadInitThunk() + 0x14 bytes(s)
0x00007FFDC672A271 (0x0000000000000000 0x0000000000000000 0x0000000000000000 0x0000000000000000), RtlUserThreadStart() + 0x21 bytes(s)