Skip to content

fsycl-host-compiler.cpp falky fails on CUDA and HIP #6760

@romanovvlad

Description

@romanovvlad

Describe the bug
https://github.com/intel/llvm-test-suite/blob/intel/SYCL/Regression/fsycl-host-compiler.cpp falky fails on CUDA and HIP
It fails, for example, here: #6759
with the message:

******************** TEST 'SYCL :: Regression/fsycl-host-compiler.cpp' FAILED ********************
Script:
--
: 'RUN: at line 1';    /__w/llvm/llvm/toolchain/bin/clang++      -fsycl -fsycl-host-compiler=g++ -DDEFINE_CHECK -fsycl-host-compiler-options="-DDEFINE_CHECK -std=c++17" -o /__w/llvm/llvm/build/SYCL/Regression/Output/fsycl-host-compiler.cpp.tmp.out /__w/llvm/llvm/llvm_test_suite/SYCL/Regression/fsycl-host-compiler.cpp
: 'RUN: at line 2';   true /__w/llvm/llvm/build/SYCL/Regression/Output/fsycl-host-compiler.cpp.tmp.out
: 'RUN: at line 3';    env SYCL_DEVICE_FILTER=ext_oneapi_cuda:gpu SYCL_PI_CUDA_ENABLE_IMAGE_SUPPORT=1  /__w/llvm/llvm/build/SYCL/Regression/Output/fsycl-host-compiler.cpp.tmp.out
: 'RUN: at line 4';   true /__w/llvm/llvm/build/SYCL/Regression/Output/fsycl-host-compiler.cpp.tmp.out
--
Exit Code: -6

Command Output (stdout):
--
$ ":" "RUN: at line 1"
note: command had no output on stdout or stderr
$ "/__w/llvm/llvm/toolchain/bin/clang++" "-fsycl" "-fsycl-host-compiler=g++" "-DDEFINE_CHECK" "-fsycl-host-compiler-options=-DDEFINE_CHECK -std=c++17" "-o" "/__w/llvm/llvm/build/SYCL/Regression/Output/fsycl-host-compiler.cpp.tmp.out" "/__w/llvm/llvm/llvm_test_suite/SYCL/Regression/fsycl-host-compiler.cpp"
# command stderr:
In file included from /__w/llvm/llvm/toolchain/bin/../include/sycl/detail/cg.hpp:14,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/handler.hpp:14,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/queue.hpp:21,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/detail/backend_traits_opencl.hpp:26,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/backend.hpp:18,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/sycl.hpp:16,
                 from /__w/llvm/llvm/llvm_test_suite/SYCL/Regression/fsycl-host-compiler.cpp:16:
/__w/llvm/llvm/toolchain/bin/../include/sycl/detail/cg_types.hpp:221:43: warning: 'interop_handler' is deprecated: interop_handler class is deprecated, use interop_handle instead with host-task [-Wdeprecated-declarations]
  221 |   std::function<void(sycl::interop_handler)> MFunc;
      |                                           ^
In file included from /__w/llvm/llvm/toolchain/bin/../include/sycl/detail/cg_types.hpp:16,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/detail/cg.hpp:14,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/handler.hpp:14,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/queue.hpp:21,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/detail/backend_traits_opencl.hpp:26,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/backend.hpp:18,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/sycl.hpp:16,
                 from /__w/llvm/llvm/llvm_test_suite/SYCL/Regression/fsycl-host-compiler.cpp:16:
/__w/llvm/llvm/toolchain/bin/../include/sycl/interop_handler.hpp:20:5: note: declared here
   20 |     interop_handler {
      |     ^~~~~~~~~~~~~~~
In file included from /__w/llvm/llvm/toolchain/bin/../include/sycl/detail/cg.hpp:14,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/handler.hpp:14,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/queue.hpp:21,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/detail/backend_traits_opencl.hpp:26,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/backend.hpp:18,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/sycl.hpp:16,
                 from /__w/llvm/llvm/llvm_test_suite/SYCL/Regression/fsycl-host-compiler.cpp:16:
/__w/llvm/llvm/toolchain/bin/../include/sycl/detail/cg_types.hpp:224:55: warning: 'interop_handler' is deprecated: interop_handler class is deprecated, use interop_handle instead with host-task [-Wdeprecated-declarations]
  224 |   InteropTask(std::function<void(sycl::interop_handler)> Func) : MFunc(Func) {}
      |                                                       ^
In file included from /__w/llvm/llvm/toolchain/bin/../include/sycl/detail/cg_types.hpp:16,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/detail/cg.hpp:14,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/handler.hpp:14,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/queue.hpp:21,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/detail/backend_traits_opencl.hpp:26,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/backend.hpp:18,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/sycl.hpp:16,
                 from /__w/llvm/llvm/llvm_test_suite/SYCL/Regression/fsycl-host-compiler.cpp:16:
/__w/llvm/llvm/toolchain/bin/../include/sycl/interop_handler.hpp:20:5: note: declared here
   20 |     interop_handler {
      |     ^~~~~~~~~~~~~~~
In file included from /__w/llvm/llvm/toolchain/bin/../include/sycl/detail/cg.hpp:14,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/handler.hpp:14,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/queue.hpp:21,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/detail/backend_traits_opencl.hpp:26,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/backend.hpp:18,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/sycl.hpp:16,
                 from /__w/llvm/llvm/llvm_test_suite/SYCL/Regression/fsycl-host-compiler.cpp:16:
/__w/llvm/llvm/toolchain/bin/../include/sycl/detail/cg_types.hpp:225:37: warning: 'interop_handler' is deprecated: interop_handler class is deprecated, use interop_handle instead with host-task [-Wdeprecated-declarations]
  225 |   void call(sycl::interop_handler &h) { MFunc(h); }
      |                                     ^
In file included from /__w/llvm/llvm/toolchain/bin/../include/sycl/detail/cg_types.hpp:16,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/detail/cg.hpp:14,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/handler.hpp:14,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/queue.hpp:21,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/detail/backend_traits_opencl.hpp:26,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/backend.hpp:18,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/sycl.hpp:16,
                 from /__w/llvm/llvm/llvm_test_suite/SYCL/Regression/fsycl-host-compiler.cpp:16:
/__w/llvm/llvm/toolchain/bin/../include/sycl/interop_handler.hpp:20:5: note: declared here
   20 |     interop_handler {
      |     ^~~~~~~~~~~~~~~
In file included from /__w/llvm/llvm/toolchain/bin/../include/sycl/queue.hpp:21,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/detail/backend_traits_opencl.hpp:26,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/backend.hpp:18,
                 from /__w/llvm/llvm/toolchain/bin/../include/sycl/sycl.hpp:16,
                 from /__w/llvm/llvm/llvm_test_suite/SYCL/Regression/fsycl-host-compiler.cpp:16:
/__w/llvm/llvm/toolchain/bin/../include/sycl/handler.hpp:1086:50: warning: 'clang::sycl_kernel' scoped attribute directive ignored [-Wattributes]
 1086 |   kernel_single_task(const KernelType &KernelFunc) {
      |                                                  ^
/__w/llvm/llvm/toolchain/bin/../include/sycl/handler.hpp:1102:69: warning: 'clang::sycl_kernel' scoped attribute directive ignored [-Wattributes]
 1102 |   kernel_single_task(const KernelType &KernelFunc, kernel_handler KH) {
      |                                                                     ^
/__w/llvm/llvm/toolchain/bin/../include/sycl/handler.hpp:1119:51: warning: 'clang::sycl_kernel' scoped attribute directive ignored [-Wattributes]
 1119 |   kernel_parallel_for(const KernelType &KernelFunc) {
      |                                                   ^
/__w/llvm/llvm/toolchain/bin/../include/sycl/handler.hpp:1135:70: warning: 'clang::sycl_kernel' scoped attribute directive ignored [-Wattributes]
 1135 |   kernel_parallel_for(const KernelType &KernelFunc, kernel_handler KH) {
      |                                                                      ^
/__w/llvm/llvm/toolchain/bin/../include/sycl/handler.hpp:1152:62: warning: 'clang::sycl_kernel' scoped attribute directive ignored [-Wattributes]
 1152 |   kernel_parallel_for_work_group(const KernelType &KernelFunc) {
      |                                                              ^
/__w/llvm/llvm/toolchain/bin/../include/sycl/handler.hpp:1169:51: warning: 'clang::sycl_kernel' scoped attribute directive ignored [-Wattributes]
 1169 |                                  kernel_handler KH) {
      |                                                   ^
In file included from /__w/llvm/llvm/toolchain/bin/../include/sycl/sycl.hpp:60,
                 from /__w/llvm/llvm/llvm_test_suite/SYCL/Regression/fsycl-host-compiler.cpp:16:
/__w/llvm/llvm/toolchain/bin/../include/sycl/ext/oneapi/backend/level_zero.hpp: In function 'T sycl::_V1::ext::oneapi::level_zero::make(const sycl::_V1::context&, typename sycl::_V1::detail::interop<sycl::_V1::backend::ext_oneapi_level_zero, T>::type, sycl::_V1::ext::oneapi::level_zero::ownership)':
/__w/llvm/llvm/toolchain/bin/../include/sycl/ext/oneapi/backend/level_zero.hpp:89:49: warning: 'sycl::_V1::queue sycl::_V1::ext::oneapi::level_zero::make_queue(const sycl::_V1::context&, pi_native_handle, bool)' is deprecated: Use make_queue with device parameter [-Wdeprecated-declarations]
   89 |                     Ownership == ownership::keep);
      |                                                 ^
/__w/llvm/llvm/toolchain/bin/../include/sycl/ext/oneapi/backend/level_zero.hpp:30:21: note: declared here
   30 | __SYCL_EXPORT queue make_queue(const context &Context,
      |                     ^~~~~~~~~~

$ ":" "RUN: at line 2"
note: command had no output on stdout or stderr
$ "true" "/__w/llvm/llvm/build/SYCL/Regression/Output/fsycl-host-compiler.cpp.tmp.out"
note: command had no output on stdout or stderr
$ ":" "RUN: at line 3"
note: command had no output on stdout or stderr
$ "env" "SYCL_DEVICE_FILTER=ext_oneapi_cuda:gpu" "SYCL_PI_CUDA_ENABLE_IMAGE_SUPPORT=1" "/__w/llvm/llvm/build/SYCL/Regression/Output/fsycl-host-compiler.cpp.tmp.out"
# command stderr:
terminate called after throwing an instance of 'sycl::_V1::runtime_error'
  what():  Native API failed. Native API returns: -42 (PI_ERROR_INVALID_BINARY) -42 (PI_ERROR_INVALID_BINARY)

error: command failed with exit status: -6

Metadata

Metadata

Assignees

No one assigned

    Labels

    bugSomething isn't workingcudaCUDA back-endhipIssues related to execution on HIP backend.

    Type

    No type

    Projects

    No projects

    Milestone

    No milestone

    Relationships

    None yet

    Development

    No branches or pull requests

    Issue actions