topic Re:CL_INVALID_KERNEL_NAME when built with -fsycl-targets=spir64_gen-unknown-unknown-sycldevice in Intel® oneAPI DPC++/C++ Compiler

CL_INVALID_KERNEL_NAME when built with -fsycl-targets=spir64_gen-unknown-unknown-sycldevice

Shukla__Gagandeep — Wed, 14 Oct 2020 16:15:00 GMT

Hi,

I'm facing a strange issue when I build my sycl code with flag -fsycl-targets=spir64_gen-unknown-unknown-sycldevice, I get exception -

Native API failed. Native API returns: -46 (CL_INVALID_KERNEL_NAME) -46 (CL_INVALID_KERNEL_NAME)

Code works fine when used without that flag but I can't do that because I have several sycl functions in my code and I get LLVM out of memory error.

I can reproduce the issue in the attached code. app.cpp contains main, lib.cpp contains a simple sycl function. When library gets compiled with -fsycl-targets or -fsycl-link-targets flag, I get the error.

Regards,
Gagan

Re:CL_INVALID_KERNEL_NAME when built with -fsycl-targets=spir64_gen-unknown-unknown-sycldevice

GouthamK_Intel — Thu, 15 Oct 2020 12:33:43 GMT

Hi Gagandeep,

We are able to reproduce the same error on our end.

Could you please try the below command? let us know the output of it.

dpcpp -c app.cpp -o app.o
dpcpp -fsycl -fsycl-targets=spir64_gen-unknown-unknown-sycldevice -Xsycl-target-backend "-device skl" lib.cpp app.o -o myout

Thanks & Regards

Goutham

Re: Re:CL_INVALID_KERNEL_NAME when built with -fsycl-targets=spir64_gen-unknown-unknown-sycldevice

Shukla__Gagandeep — Thu, 15 Oct 2020 15:44:16 GMT

Hi Gautham,

The command you gave works but my issue is that in my actual project, I'm using CMake as build tool. There are many libraries that get compiled individually and then get linked with application binary.

The sample code + cmake files that I gave actually replicate my build process along with the issue I face and I have to solve this issue within those constraints. I can not directly compile files on command line

Regards,
Gagan

Re:CL_INVALID_KERNEL_NAME when built with -fsycl-targets=spir64_gen-unknown-unknown-sycldevice

GouthamK_Intel — Wed, 21 Oct 2020 11:49:33 GMT

Hi Gagan,

We are working on your issue. We will get back to you soon.

Regards

Goutham

Re: CL_INVALID_KERNEL_NAME when built with -fsycl-targets=spir64_gen-unknown-unknown-sycldevice

GouthamK_Intel — Fri, 23 Oct 2020 13:45:58 GMT

Hi Gagan,

We have analysed your CMake configuration, we observed that there are some issues during the linking stage. you need to provide the -fsycl-targets and Xsycl-target-backend during the linking stage too.

So you can try providing -fsycl-targets and -Xs to cmake exe linker flag.

Command:

cmake -DCMAKE_EXE_LINKER_FLAGS='-fsycl-targets=spir64_gen-unknown-unknown-sycldevice -Xs "-device kbl"' ..

Let us know if you face any further issues.

Have a Good day!

Thanks & Regards

Goutham

Re: CL_INVALID_KERNEL_NAME when built with -fsycl-targets=spir64_gen-unknown-unknown-sycldevice

Shukla__Gagandeep — Sat, 24 Oct 2020 16:21:49 GMT

Hi Gautham,

The solution you provided worked with the test code that I shared with you but when I added the same to my actual code, it failed at link stage. Error I get is:

[100%] Linking CXX executable ../../bin/cycles InvalidFunctionCall: Unexpected llvm intrinsic: llvm.exp.f32 [Src: /netbatch/donb1852340_00/runDir/09/20200827_000000/llvm/llvm-spirv/lib/SPIRV/SPIRVWriter.cpp:2358 ] dpcpp: error: llvm-spirv command failed with exit code 6 (use -v to see invocation) src/app/CMakeFiles/cycles.dir/build.make:221: recipe for target 'bin/cycles' failed make[2]: *** [bin/cycles] Error 6 CMakeFiles/Makefile2:510: recipe for target 'src/app/CMakeFiles/cycles.dir/all' failed make[1]: *** [src/app/CMakeFiles/cycles.dir/all] Error 2 Makefile:148: recipe for target 'all' failed make: *** [all] Error 2

I added

add_compile_options( -fsycl-targets=spir64_gen-unknown-unknown-sycldevice )

To my library that contains OneAPI code, cleaned up my build folder and used the command you provided to run cmake.

If I build oneapi library without above compile option, I get following error:

[100%] Linking CXX executable ../../bin/cycles llvm-link: Not enough positional command line arguments specified! Must specify at least 1 positional argument: See: /home/kuljeet/intel/oneapi/compiler/2021.1-beta09/linux/bin/llvm-link --help dpcpp: error: sycl-link command failed with exit code 1 (use -v to see invocation) src/app/CMakeFiles/cycles.dir/build.make:221: recipe for target 'bin/cycles' failed make[2]: *** [bin/cycles] Error 1 CMakeFiles/Makefile2:510: recipe for target 'src/app/CMakeFiles/cycles.dir/all' failed make[1]: *** [src/app/CMakeFiles/cycles.dir/all] Error 2 Makefile:148: recipe for target 'all' failed make: *** [all] Error 2

I'm not even sure what else to try.

Regards,
Gagan

Re: CL_INVALID_KERNEL_NAME when built with -fsycl-targets=spir64_gen-unknown-unknown-sycldevice

GouthamK_Intel — Mon, 26 Oct 2020 08:31:57 GMT

Hi Gagan,

Could you please try adding -Xsycl-target-backend along with -fsycl-targets in add_compile_options.

-Xsycl-target-backend "-device skl" // Device depending on your hardware, e.g., skl

If you still face any errors, please provide the logs of CMake with verbose ON.

cmake -DCMAKE_EXE_LINKER_FLAGS='-fsycl-targets=spir64_gen-unknown-unknown-sycldevice -Xs "-device skl"' -DCMAKE_VERBOSE_MAKEFILE:BOOL=ON .. make V=1

Also, provide the details of the device for which you are targeting.

Regards

Goutham

Re: CL_INVALID_KERNEL_NAME when built with -fsycl-targets=spir64_gen-unknown-unknown-sycldevice

Shukla__Gagandeep — Tue, 27 Oct 2020 09:08:56 GMT

Hi Gautham,

I'm still getting the error:

InvalidFunctionCall: Unexpected llvm intrinsic: llvm.exp.f32 [Src: /netbatch/donb1852340_00/runDir/09/20200827_000000/llvm/llvm-spirv/lib/SPIRV/SPIRVWriter.cpp:2358 ] dpcpp: error: llvm-spirv command failed with exit code 6 (use -v to see invocation) make[2]: *** [bin/cycles] Error 6 make[1]: *** [src/app/CMakeFiles/cycles.dir/all] Error 2 make: *** [all] Error 2

Attached zip contains cmake and make log.

Target device info:

platform_name : Intel(R) OpenCL HD Graphics platform_version : OpenCL 2.1 platform_vendor : Intel(R) Corporation vendor_name : Intel(R) Gen9 HD Graphics NEO vendor_id : 32902 vendor : Intel(R) Corporation driver_version : 20.28.17293 version : OpenCL 2.1 NEO opencl_c_version : OpenCL C 2.0

Regards,
Gagan

Re:CL_INVALID_KERNEL_NAME when built with -fsycl-targets=spir64_gen-unknown-unknown-sycldevice

GouthamK_Intel — Wed, 28 Oct 2020 10:27:14 GMT

Hi Gagan,

From the logs that you have attached it is little difficult to pinpoint the exact issue. It would be helpful if you can isolate the exact issue you are facing and provide a small reproducer of it.

Also, provide steps to reproduce the exact issue you are facing if possible.

Thanks & Regards

Goutham

Re: Re:CL_INVALID_KERNEL_NAME when built with -fsycl-targets=spir64_gen-unknown-unknown-sycldevice

Shukla__Gagandeep — Mon, 02 Nov 2020 20:55:58 GMT

Hi Gautham,

Please find attached sample workspace which can reproduce the error I am facing.

Steps to reproduce are:

cmake -DCMAKE_EXE_LINKER_FLAGS='-fsycl-targets=spir64_gen-unknown-unknown-sycldevice -Xsycl-target-backend "-device skl"' .. make

and the error I get is:

InvalidFunctionCall: Unexpected llvm intrinsic: llvm.ctpop.i32 [Src: /netbatch/donb1852340_00/runDir/09/20200827_000000/llvm/llvm-spirv/lib/SPIRV/SPIRVWriter.cpp:2358 ] dpcpp: error: llvm-spirv command failed with exit code 6 (use -v to see invocation) app/CMakeFiles/test_app.dir/build.make:103: recipe for target 'app/test_app' failed make[2]: *** [app/test_app] Error 6 CMakeFiles/Makefile2:133: recipe for target 'app/CMakeFiles/test_app.dir/all' failed make[1]: *** [app/CMakeFiles/test_app.dir/all] Error 2 Makefile:102: recipe for target 'all' failed make: *** [all] Error 2

Regards,
Gagan

Re:CL_INVALID_KERNEL_NAME when built with -fsycl-targets=spir64_gen-unknown-unknown-sycldevice

GouthamK_Intel — Tue, 03 Nov 2020 07:36:45 GMT

Hi Gagan,

Thanks for the reproducer. We are able to reproduce it on beta09.

However, since beta10 has released, could you please give it a try and let us know if you face any issues.

Also, please do migrate the entire application with beta10 dpct and compile it.

Thanks & Regards

Goutham

Re: Re:CL_INVALID_KERNEL_NAME when built with -fsycl-targets=spir64_gen-unknown-unknown-sycldevice

Shukla__Gagandeep — Thu, 05 Nov 2020 20:17:37 GMT

Hi Gautham,

I tried converting code using beta10. It has not converted any of the cuda bring up functions like cuInit, cuDeviceGet, cuDeviceGetAttribute, cuMemInfo, cuMemAlloc, cuMemHostAlloc, cuTexObjectCreate .... etc. Datatype conversion across files from intX, floatX to sycl::intX, sycl::floatX has been missed at several places.

And my old code is not even compiling. beta10 is not recognizing dpct::image_info, dpct::image_base_p or dpct::create_image(), dpct::image_accessor, ~image_base().

Regards,
Gagan

Re:CL_INVALID_KERNEL_NAME when built with -fsycl-targets=spir64_gen-unknown-unknown-sycldevice

GouthamK_Intel — Tue, 10 Nov 2020 11:14:10 GMT

Hi Gagandeep,

Thanks for reporting the issue, we are able to reproduce the error which you are facing.

We are forwarding this thread to the concerned internal team.

Thanks & Regards

Goutham

Re: Re:CL_INVALID_KERNEL_NAME when built with -fsycl-targets=spir64_gen-unknown-unknown-sycldevice

Shukla__Gagandeep — Tue, 10 Nov 2020 18:50:14 GMT

Hi,

Update with beta10:

I was able to resolve all the API changes that are done in beta 10 and result of compilation is still the same. I get following error

[100%] Linking CXX executable ../../bin/cycles InvalidFunctionCall: Unexpected llvm intrinsic: llvm.ctpop.i32 [Src: /netbatch/donb2965411_00/runDir/88/20201005_160000/llvm/llvm-spirv/lib/SPIRV/SPIRVWriter.cpp:2399 ] dpcpp: error: llvm-spirv command failed with exit code 6 (use -v to see invocation) src/app/CMakeFiles/cycles.dir/build.make:221: recipe for target 'bin/cycles' failed make[2]: *** [bin/cycles] Error 6 CMakeFiles/Makefile2:510: recipe for target 'src/app/CMakeFiles/cycles.dir/all' failed make[1]: *** [src/app/CMakeFiles/cycles.dir/all] Error 2 Makefile:148: recipe for target 'all' failed make: *** [all] Error 2

when compiled with

cmake -DCMAKE_EXE_LINKER_FLAGS='-fsycl-targets=spir64_gen-unknown-unknown-sycldevice -Xsycl-target-backend "-device skl"' ..

If there is any thing I can try in the mean time, please let me know.

Regards,
Gagan

Re:CL_INVALID_KERNEL_NAME when built with -fsycl-targets=spir64_gen-unknown-unknown-sycldevice

Sravani_K_Intel — Tue, 10 Nov 2020 19:19:43 GMT

Hi Gagandeep,

Please try compiling with the flag -fno-sycl-early-optimizations.

There is a known issue in Beta10 which is causing this error for some intrinsics and ctpop is one of them.

Re: Re:CL_INVALID_KERNEL_NAME when built with -fsycl-targets=spir64_gen-unknown-unknown-sycldevice

Shukla__Gagandeep — Mon, 16 Nov 2020 09:05:01 GMT

Now the error is

InvalidFunctionCall: Unexpected llvm intrinsic: llvm.exp.f32 [Src: /netbatch/donb2965411_00/runDir/88/20201005_160000/llvm/llvm-spirv/lib/SPIRV/SPIRVWriter.cpp:2399 ] dpcpp: error: llvm-spirv command failed with exit code 6 (use -v to see invocation) src/app/CMakeFiles/cycles.dir/build.make:220: recipe for target 'bin/cycles' failed make[2]: *** [bin/cycles] Error 6 CMakeFiles/Makefile2:509: recipe for target 'src/app/CMakeFiles/cycles.dir/all' failed make[1]: *** [src/app/CMakeFiles/cycles.dir/all] Error 2 Makefile:148: recipe for target 'all' failed make: *** [all] Error 2

Regards,
Gagan

Re:CL_INVALID_KERNEL_NAME when built with -fsycl-targets=spir64_gen-unknown-unknown-sycldevice

Sravani_K_Intel — Tue, 16 Feb 2021 18:56:04 GMT

Hi Gagan,

Sorry for the delayed response.

Did you get a chance to verify this with the DPC++ Compiler from the oneAPI Gold release? If you still have issues, please attach the reproducer after migrating with Intel(R) DPC++ Compatibility Tool version 2021.1.

Thank you.

Re:CL_INVALID_KERNEL_NAME when built with -fsycl-targets=spir64_gen-unknown-unknown-sycldevice

Sravani_K_Intel — Wed, 24 Feb 2021 18:01:09 GMT

This issue has been resolved and we will no longer respond to this thread. If you require additional assistance from Intel, please start a new thread. Any further interaction in this thread will be considered community only