-
Notifications
You must be signed in to change notification settings - Fork 809
[SYCL] Fix handling of mem_channel buffer property #9203
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
Conversation
This commit fixes the sycl::property::buffer::mem_channel handling when creating a buffer with the property. Additionally it fixes the associated device info query and aspect check. Signed-off-by: Larsen, Steffen <steffen.larsen@intel.com>
sarnex
left a comment
There was a problem hiding this comment.
Choose a reason for hiding this comment
The reason will be displayed to describe this comment to others. Learn more.
esimd lgtm
| if (ParamName == PI_EXT_INTEL_DEVICE_INFO_MEM_CHANNEL_SUPPORT) { | ||
| ReturnHelper ReturnValue(ParamValueSize, ParamValue, ParamValueSizeRet); | ||
| return ReturnValue(pi_bool{false}); | ||
| } |
There was a problem hiding this comment.
Choose a reason for hiding this comment
The reason will be displayed to describe this comment to others. Learn more.
@smaslov-intel - I did a similar work-around in #8954. Is there a better way of doing it?
There was a problem hiding this comment.
Choose a reason for hiding this comment
The reason will be displayed to describe this comment to others. Learn more.
@steffenlarsen : Yes, let's not add new stuff here.
Please temporary add UR extension here:
| // TODO: promote all of the below extensions to the Unified Runtime |
And note @kbenzie to promote it into UR.
The the handling would naturally go into https://github.com/intel/llvm/blob/sycl/sycl/plugins/unified_runtime/ur/adapters/level_zero/ur_level_zero.cpp
There was a problem hiding this comment.
Choose a reason for hiding this comment
The reason will be displayed to describe this comment to others. Learn more.
I was not aware of this list of constants until now. Do lines 23-57 encapsulate these UR_EXT_* symbols or are there additional ones?
There was a problem hiding this comment.
Choose a reason for hiding this comment
The reason will be displayed to describe this comment to others. Learn more.
Found oneapi-src/unified-runtime#374 which seems to cover theses, added mention of this.
npmiller
left a comment
There was a problem hiding this comment.
Choose a reason for hiding this comment
The reason will be displayed to describe this comment to others. Learn more.
cuda and hip LGTM
Signed-off-by: Larsen, Steffen <steffen.larsen@intel.com>
Signed-off-by: Larsen, Steffen <steffen.larsen@intel.com>
Signed-off-by: Larsen, Steffen <steffen.larsen@intel.com>
smaslov-intel
left a comment
There was a problem hiding this comment.
Choose a reason for hiding this comment
The reason will be displayed to describe this comment to others. Learn more.
LGTM
intel#9203 Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
intel#9203 Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
intel#9203 Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
intel#9203 Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
This commit fixes the sycl::property::buffer::mem_channel handling when creating a buffer with the property. Additionally it fixes the associated device info query and aspect check. --------- Signed-off-by: Larsen, Steffen <steffen.larsen@intel.com>
This commit fixes the sycl::property::buffer::mem_channel handling when creating a buffer with the property. Additionally it fixes the associated device info query and aspect check.