Skip to content

[SYCL][Fusion] Error if fusion unsupported on device #12171

New issue

Have a question about this project? Sign up for a free GitHub account to open an issue and contact its maintainers and the community.

By clicking “Sign up for GitHub”, you agree to our terms of service and privacy statement. We’ll occasionally send you account related emails.

Already on GitHub? Sign in to your account

Merged

Conversation

sommerlukas
Copy link
Contributor

@sommerlukas sommerlukas commented Dec 14, 2023

The kernel fusion extension document says that an error will be thrown if a queue is constructed with sycl::ext::codeplay::experimental::property::queue::enable_fusion, but the underlying device does not support fusion (i.e., returns false for get_info<sycl::ext::codeplay::experimental::info::device::supports_fusion>()). This change implements this behavior.

Also, kernel fusion is currently not supported for SYCL devices of device type accelerator, as devices such as FPGAs do not support JIT compilation at runtime. Therefore, mark all end-to-end tests related to kernel fusion as unsupported for devices of type accelerator.

In addition, use the newly created file to make the fact that kernel fusion is currently unsupported on Windows more explicit.

Kernel fusion is currently not supported for SYCL devices of device type
accelerator, as devices such as FPGAs do not support JIT compilation at
runtime.

Mark all end-to-end tests related to kernel fusion as unsupported for
devices of type accelerator.

Also use the newly created file to make the fact that kernel fusion is
currently unsupported on Windows more explicit.

Signed-off-by: Lukas Sommer <[email protected]>
@sommerlukas sommerlukas self-assigned this Dec 14, 2023
@sommerlukas sommerlukas requested a review from a team as a code owner December 14, 2023 10:23
@sommerlukas sommerlukas requested a review from a team as a code owner December 14, 2023 17:07
@sommerlukas sommerlukas changed the title [SYCL][Fusion] Mark unsupported on accelerator [SYCL][Fusion] Error if fusion unsupported on device Dec 14, 2023
@sommerlukas sommerlukas requested a review from jopperm December 14, 2023 17:10
Copy link
Contributor

@maarquitos14 maarquitos14 left a comment

Choose a reason for hiding this comment

The reason will be displayed to describe this comment to others. Learn more.

LGTM.

Refine fusion device info to not report support for accelerator devices
on the OpenCL backend.

Signed-off-by: Lukas Sommer <[email protected]>
@sommerlukas sommerlukas requested a review from a team as a code owner December 15, 2023 09:27
Copy link
Contributor

@EwanC EwanC left a comment

Choose a reason for hiding this comment

The reason will be displayed to describe this comment to others. Learn more.

LGTM

Signed-off-by: Lukas Sommer <[email protected]>
@dm-vodopyanov dm-vodopyanov merged commit 70f0835 into intel:sycl Dec 15, 2023
@sommerlukas sommerlukas deleted the mark-fusion-unsupported-accelerator branch December 15, 2023 13:51
Sign up for free to join this conversation on GitHub. Already have an account? Sign in to comment
Labels
None yet
Projects
None yet
Development

Successfully merging this pull request may close these issues.

5 participants