[SYCL] Implement DeviceKernelInfo for interop kernels #20020

vinser52 · 2025-09-09T16:02:16Z

For kernels represented by user-provided functors/lambdas the DeviceKernelInfo is stored in the ProgramManager::m_DeviceKernelInfoMap.
This PR introduces support for the DeviceKernelInfo for interop kernels.

vinser52 · 2025-09-09T16:05:48Z

This PR is required by #19843.

sycl/source/detail/kernel_impl.hpp

sycl/source/detail/kernel_impl.cpp

sycl/source/detail/kernel_impl.hpp

Co-authored-by: Andrei Elovikov <[email protected]>

sycl/source/handler.cpp

sycl/source/detail/kernel_impl.cpp

uditagarwal97 · 2025-09-11T02:16:18Z

fyi, Jenkins CI failure is related:

[2025-09-10T23:23:54.591Z] /rdrive/ref/gcc/7.5.0/rhel70/efi2/bin/g++ -DCL_TARGET_OPENCL_VERSION=300 -DCL_USE_DEPRECATED_OPENCL_1_2_APIS=1 -DEXPERIMENTAL_KEY_INSTRUCTIONS -DSYCL2020_DISABLE_DEPRECATION_WARNINGS -DSYCL_EXT_JIT_ENABLE -DSYCL_RT_ZSTD_AVAILABLE -DXPTI_ENABLE_INSTRUMENTATION -DXPTI_STATIC_LIBRARY -D_DEBUG -D_GLIBCXX_ASSERTIONS -D_GNU_SOURCE -D__DPCPP_ENABLE_UNFINISHED_KHR_EXTENSIONS -D__STDC_CONSTANT_MACROS -D__STDC_FORMAT_MACROS -D__STDC_LIMIT_MACROS -D__SYCL_INTERNAL_API -I/netbatch/donb25783_00/runDir/jenkins-dir/workspace/SYCL_CI/intel/Build_PR_RHEL/llvm.obj/tools/sycl/source -I/netbatch/donb25783_00/runDir/jenkins-dir/workspace/SYCL_CI/intel/Build_PR_RHEL/llvm.src/sycl/source -I/netbatch/donb25783_00/runDir/jenkins-dir/workspace/SYCL_CI/intel/Build_PR_RHEL/llvm.obj/include -I/netbatch/donb25783_00/runDir/jenkins-dir/workspace/SYCL_CI/intel/Build_PR_RHEL/llvm.src/llvm/include -I/netbatch/donb25783_00/runDir/jenkins-dir/workspace/SYCL_CI/intel/Build_PR_RHEL/llvm.src/xpti/include -I/netbatch/donb25783_00/runDir/jenkins-dir/workspace/SYCL_CI/intel/Build_PR_RHEL/llvm.src/sycl/include -I/netbatch/donb25783_00/runDir/jenkins-dir/workspace/SYCL_CI/intel/Build_PR_RHEL/llvm.src/sycl-jit/common/include -I/netbatch/donb25783_00/runDir/jenkins-dir/workspace/SYCL_CI/intel/Build_PR_RHEL/llvm.src/sycl-jit/jit-compiler/include -I/netbatch/donb25783_00/runDir/jenkins-dir/workspace/SYCL_CI/intel/Build_PR_RHEL/llvm.src/unified-runtime/include -I/netbatch/donb25783_00/runDir/jenkins-dir/workspace/SYCL_CI/intel/Build_PR_RHEL/llvm.obj/_deps/ocl-headers-src -isystem /netbatch/donb25783_00/runDir/jenkins-dir/workspace/SYCL_CI/intel/Build_PR_RHEL/llvm.obj/_deps/emhash-src -fPIC -fno-semantic-interposition -fvisibility-inlines-hidden -Werror=date-time -fno-lifetime-dse -Wall -Wextra -Wno-unused-parameter -Wwrite-strings -Wcast-qual -Wno-missing-field-initializers -pedantic -Wno-long-long -Wimplicit-fallthrough -Wno-uninitialized -Wno-nonnull -Wno-noexcept-type -Wdelete-non-virtual-dtor -Wno-comment -Wno-misleading-indentation -fdiagnostics-color -ffunction-sections -fdata-sections -Wall -Wextra -Werror -O3 -DNDEBUG -UNDEBUG -ffunction-sections -fdata-sections -fvisibility=hidden -fvisibility-inlines-hidden -Wno-psabi -std=c++1z -MD -MT tools/sycl/source/CMakeFiles/sycl_object.dir/detail/kernel_impl.cpp.o -MF tools/sycl/source/CMakeFiles/sycl_object.dir/detail/kernel_impl.cpp.o.d -o tools/sycl/source/CMakeFiles/sycl_object.dir/detail/kernel_impl.cpp.o -c /netbatch/donb25783_00/runDir/jenkins-dir/workspace/SYCL_CI/intel/Build_PR_RHEL/llvm.src/sycl/source/detail/kernel_impl.cpp

[2025-09-10T23:23:54.591Z] /netbatch/donb25783_00/runDir/jenkins-dir/workspace/SYCL_CI/intel/Build_PR_RHEL/llvm.src/sycl/source/detail/kernel_impl.cpp: In constructor ‘sycl::_V1::detail::kernel_impl::kernel_impl(sycl::_V1::detail::Managed<ur_kernel_handle_t_*>&&, sycl::_V1::detail::context_impl&, sycl::_V1::detail::kernel_bundle_impl*, const KernelArgMask*)’:
[2025-09-10T23:23:54.591Z] /netbatch/donb25783_00/runDir/jenkins-dir/workspace/SYCL_CI/intel/Build_PR_RHEL/llvm.src/sycl/source/detail/kernel_impl.cpp:31:55: internal compiler error: in replace_placeholders_r, at cp/tree.c:2804
[2025-09-10T23:23:54.591Z]        MDeviceKernelInfo(MInteropDeviceKernelInfoHolder) {
[2025-09-10T23:23:54.591Z]                                                        ^
[2025-09-10T23:23:54.591Z] 0x6a5d75 replace_placeholders_r
[2025-09-10T23:23:54.591Z] 	../../gcc-7.5.0/gcc/cp/tree.c:2804
[2025-09-10T23:23:54.591Z] 0xd01fa5 walk_tree_1(tree_node**, tree_node* (*)(tree_node**, int*, void*), void*, hash_set<tree_node*, default_hash_traits<tree_node*> >*, tree_node* (*)(tree_node**, int*, tree_node* (*)(tree_node**, int*, void*), void*, hash_set<tree_node*, default_hash_traits<tree_node*> >*))
[2025-09-10T23:23:54.591Z] 	../../gcc-7.5.0/gcc/tree.c:11839
[2025-09-10T23:23:54.591Z] 0x6a5c53 replace_placeholders_r
[2025-09-10T23:23:54.591Z] 	../../gcc-7.5.0/gcc/cp/tree.c:2839
[2025-09-10T23:23:54.591Z] 0xd01fa5 walk_tree_1(tree_node**, tree_node* (*)(tree_node**, int*, void*), void*, hash_set<tree_node*, default_hash_traits<tree_node*> >*, tree_node* (*)(tree_node**, int*, tree_node* (*)(tree_node**, int*, void*), void*, hash_set<tree_node*, default_hash_traits<tree_node*> >*))
[2025-09-10T23:23:54.591Z] 	../../gcc-7.5.0/gcc/tree.c:11839
[2025-09-10T23:23:54.591Z] 0xd02414 walk_tree_1(tree_node**, tree_node* (*)(tree_node**, int*, void*), void*, hash_set<tree_node*, default_hash_traits<tree_node*> >*, tree_node* (*)(tree_node**, int*, tree_node* (*)(tree_node**, int*, void*), void*, hash_set<tree_node*, default_hash_traits<tree_node*> >*))
[2025-09-10T23:23:54.591Z] 	../../gcc-7.5.0/gcc/tree.c:12066
[2025-09-10T23:23:54.591Z] 0x6a5c53 replace_placeholders_r
[2025-09-10T23:23:54.591Z] 	../../gcc-7.5.0/gcc/cp/tree.c:2839
[2025-09-10T23:23:54.591Z] 0xd01fa5 walk_tree_1(tree_node**, tree_node* (*)(tree_node**, int*, void*), void*, hash_set<tree_node*, default_hash_traits<tree_node*> >*, tree_node* (*)(tree_node**, int*, tree_node* (*)(tree_node**, int*, void*), void*, hash_set<tree_node*, default_hash_traits<tree_node*> >*))
[2025-09-10T23:23:54.591Z] 	../../gcc-7.5.0/gcc/tree.c:11839
[2025-09-10T23:23:54.591Z] 0xd02414 walk_tree_1(tree_node**, tree_node* (*)(tree_node**, int*, void*), void*, hash_set<tree_node*, default_hash_traits<tree_node*> >*, tree_node* (*)(tree_node**, int*, tree_node* (*)(tree_node**, int*, void*), void*, hash_set<tree_node*, default_hash_traits<tree_node*> >*))
[2025-09-10T23:23:54.591Z] 	../../gcc-7.5.0/gcc/tree.c:12066
[2025-09-10T23:23:54.591Z] 0x6a9093 replace_placeholders(tree_node*, tree_node*, bool*)
[2025-09-10T23:23:54.591Z] 	../../gcc-7.5.0/gcc/cp/tree.c:2877
[2025-09-10T23:23:54.591Z] 0x6d110d cp_gimplify_init_expr
[2025-09-10T23:23:54.591Z] 	../../gcc-7.5.0/gcc/cp/cp-gimplify.c:500
[2025-09-10T23:23:54.591Z] 0x6d110d cp_gimplify_expr(tree_node**, gimple**, gimple**)
[2025-09-10T23:23:54.591Z] 	../../gcc-7.5.0/gcc/cp/cp-gimplify.c:659
[2025-09-1T23:23:54.591Z] 0x8e0285 gimplify_expr(tree_node**, gimple**, gimple**, bool (*)(tree_node*), int)
[2025-09-10T23:23:54.591Z] 	../../gcc-7.5.0/gcc/gimplify.c:11232
[2025-09-10T23:23:54.591Z] 0x8e3b98 gimplify_stmt(tree_node**, gimple**)
[2025-09-10T23:23:54.591Z] 	../../gcc-7.5.0/gcc/gimplify.c:6526
[2025-09-10T23:23:54.591Z] 0x8e2066 gimplify_cleanup_point_expr
[2025-09-10T23:23:54.591Z] 	../../gcc-7.5.0/gcc/gimplify.c:6269
[2025-09-10T23:23:54.591Z] 0x8e2066 gimplify_expr(tree_node**, gimple**, gimple**, bool (*)(tree_node*), int)
[2025-09-10T23:3:54.591Z] 	../../gcc-7.5.0/gcc/gimplify.c:11699
[2025-09-10T23:23:54.591Z] 0x8e3b98 gimplify_stmt(tree_node**, gimple**)
[2025-09-10T23:23:54.591Z] 	../../gcc-7.5.0/gcc/gimplify.c:6526
[2025-09-10T23:23:54.591Z] 0x8e1dbb gimplify_statement_list
[2025-09-10T23:23:54.591Z] 	../../gcc-7.5.0/gcc/gimplify.c:1721
[2025-09-10T23:23:54.591Z] 0x8e1dbb gimplify_expr(tree_node**, gimple**, gimple**, bool (*)(tree_node*), int)
[2025-09-10T23:23:54.591Z] 	../../gcc-7.5.0/gcc/gimplify.c:11751
[2025-09-10T23:23:54.592Z] 0x8e3b98 gimplify_stmt(tree_node**, gimple**)
[2025-09-10T23:23:54.592Z] 	../../gcc-7.5.0/gcc/gimplify.c:6526
[2025-09-10T23:23:54.592Z] 0x8e1e9b gimplify_and_add(tree_node*, gimple**)
[2025-09-10T23:23:54.592Z] 	../../gcc-7.5.0/gcc/gimplify.c:436
[2025-09-10T23:23:54.592Z] Please submit a full bug report,
[2025-09-10T23:23:54.592Z] with preprocessed source if appropriate.
[2025-09-10T23:23:54.592Z] Please include the complete backtrace with any bug report.

Maybe you need a workaround like #20035

vinser52 requested a review from a team as a code owner September 9, 2025 16:02

vinser52 requested a review from cperkinsintel September 9, 2025 16:02

vinser52 had a problem deploying to WindowsCILock September 9, 2025 16:02 — with GitHub Actions Failure

vinser52 requested review from sergey-semenov and aelovikov-intel September 9, 2025 16:03

aelovikov-intel reviewed Sep 9, 2025

View reviewed changes

sycl/source/detail/kernel_impl.hpp Outdated Show resolved Hide resolved

vinser52 had a problem deploying to WindowsCILock September 9, 2025 17:03 — with GitHub Actions Failure

vinser52 mentioned this pull request Sep 9, 2025

[SYCL] Fix compile time info initialization #20003

Merged

cperkinsintel reviewed Sep 9, 2025

View reviewed changes

sycl/source/detail/kernel_impl.hpp Outdated Show resolved Hide resolved

vinser52 had a problem deploying to WindowsCILock September 10, 2025 09:11 — with GitHub Actions Failure

vinser52 had a problem deploying to WindowsCILock September 10, 2025 09:37 — with GitHub Actions Failure

vinser52 added 2 commits September 10, 2025 12:48

Implement DeviceKernelInfo for interop kernels

3758e75

Address review comment

ce66c47

vinser52 force-pushed the device_kernel_info_interop branch from 7bb01f1 to ce66c47 Compare September 10, 2025 10:52

vinser52 temporarily deployed to WindowsCILock September 10, 2025 10:52 — with GitHub Actions Inactive

vinser52 had a problem deploying to WindowsCILock September 10, 2025 11:21 — with GitHub Actions Failure

vinser52 added 2 commits September 10, 2025 13:46

Update Linux symbols

4ac3937

Do not set the DeviceKernelInfo twice

59984ce

vinser52 had a problem deploying to WindowsCILock September 10, 2025 13:37 — with GitHub Actions Error

aelovikov-intel reviewed Sep 10, 2025

View reviewed changes

sycl/source/detail/kernel_impl.cpp Outdated Show resolved Hide resolved

aelovikov-intel reviewed Sep 10, 2025

View reviewed changes

sycl/source/detail/kernel_impl.hpp Outdated Show resolved Hide resolved

Update sycl/source/detail/kernel_impl.hpp

2f84b15

Co-authored-by: Andrei Elovikov <[email protected]>

aelovikov-intel reviewed Sep 10, 2025

View reviewed changes

sycl/source/handler.cpp Outdated Show resolved Hide resolved

vinser52 temporarily deployed to WindowsCILock September 10, 2025 13:45 — with GitHub Actions Inactive

vinser52 temporarily deployed to WindowsCILock September 10, 2025 14:12 — with GitHub Actions Inactive

vinser52 had a problem deploying to WindowsCILock September 10, 2025 14:12 — with GitHub Actions Failure

vinser52 temporarily deployed to WindowsCILock September 10, 2025 14:44 — with GitHub Actions Inactive

vinser52 had a problem deploying to WindowsCILock September 10, 2025 15:12 — with GitHub Actions Failure

Merge branch 'sycl' into device_kernel_info_interop

a40cff7

vinser52 had a problem deploying to WindowsCILock September 10, 2025 17:19 — with GitHub Actions Error

Adress review comment

9059f38

vinser52 had a problem deploying to WindowsCILock September 10, 2025 17:24 — with GitHub Actions Error

Address review comment

c53232c

vinser52 temporarily deployed to WindowsCILock September 10, 2025 17:26 — with GitHub Actions Inactive

aelovikov-intel reviewed Sep 10, 2025

View reviewed changes

sycl/source/detail/kernel_impl.cpp Outdated Show resolved Hide resolved

aelovikov-intel reviewed Sep 10, 2025

View reviewed changes

sycl/source/detail/kernel_impl.cpp Outdated Show resolved Hide resolved

Address review comment

914b54d

vinser52 temporarily deployed to WindowsCILock September 10, 2025 18:14 — with GitHub Actions Inactive

vinser52 had a problem deploying to WindowsCILock September 10, 2025 18:14 — with GitHub Actions Error

vinser52 temporarily deployed to WindowsCILock September 10, 2025 18:27 — with GitHub Actions Inactive

vinser52 temporarily deployed to WindowsCILock September 10, 2025 19:09 — with GitHub Actions Inactive

Address review comments

88dc093

vinser52 temporarily deployed to WindowsCILock September 10, 2025 21:16 — with GitHub Actions Inactive

vinser52 requested a review from aelovikov-intel September 10, 2025 21:17

aelovikov-intel approved these changes Sep 10, 2025

View reviewed changes

vinser52 temporarily deployed to WindowsCILock September 10, 2025 21:49 — with GitHub Actions Inactive

Fix Jenkins issue

0cbc130

vinser52 temporarily deployed to WindowsCILock September 11, 2025 09:26 — with GitHub Actions Inactive

vinser52 temporarily deployed to WindowsCILock September 11, 2025 09:53 — with GitHub Actions Inactive

Possible fix for Jenkins

3333734

vinser52 requested a deployment to WindowsCILock September 11, 2025 10:55 — with GitHub Actions In progress

Provide feedback

Saved searches

Use saved searches to filter your results more quickly

Uh oh!

[SYCL] Implement DeviceKernelInfo for interop kernels #20020

[SYCL] Implement DeviceKernelInfo for interop kernels #20020

vinser52 commented Sep 9, 2025

Uh oh!

vinser52 commented Sep 9, 2025

Uh oh!

Uh oh!

Uh oh!

Uh oh!

Uh oh!

Uh oh!

Uh oh!

Uh oh!

uditagarwal97 commented Sep 11, 2025

Uh oh!

Uh oh!

[SYCL] Implement DeviceKernelInfo for interop kernels #20020

Are you sure you want to change the base?

[SYCL] Implement DeviceKernelInfo for interop kernels #20020

Conversation

vinser52 commented Sep 9, 2025

Uh oh!

vinser52 commented Sep 9, 2025

Uh oh!

Uh oh!

Uh oh!

Uh oh!

Uh oh!

Uh oh!

Uh oh!

Uh oh!

uditagarwal97 commented Sep 11, 2025

Uh oh!

Uh oh!