Skip to content

Add __SYCL_EXPORT to declaration of contextSetExtendedDeleter #1531

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
merged 2 commits into from
Apr 20, 2020

Conversation

nyalloc
Copy link
Contributor

@nyalloc nyalloc commented Apr 16, 2020

Bug fix. __SYCL_EXPORT attribute missing from contextSetExtendedDeleter definition, meaning it was not publically visible.

Signed-off-by: Stuart Adams <stuart.adams@codeplay.com>
@nyalloc nyalloc force-pushed the stuart/export_contextSetExtendedDeleter branch from db77c55 to 3126f99 Compare April 16, 2020 11:56
Signed-off-by: Stuart Adams <stuart.adams@codeplay.com>
void contextSetExtendedDeleter(const cl::sycl::context &constext,
pi_context_extended_deleter func,
void *user_data);
__SYCL_EXPORT void contextSetExtendedDeleter(const cl::sycl::context &constext,
Copy link
Contributor

Choose a reason for hiding this comment

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

I don't see any users of it. Why does this need to be exported from libsycl?

Copy link
Contributor

Choose a reason for hiding this comment

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

Please also document the recently added PI API: piextContextSetExtendedDeleter in pi.h

Copy link
Contributor

Choose a reason for hiding this comment

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

Why is it not implemented for OpenCL?

Copy link
Contributor Author

Choose a reason for hiding this comment

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

Hi, this function is used in the cuBLAS backend to OneMKL. If it isn't exported, the cuBLAS backend does not work.

uxlfoundation/oneMath#2 (comment)

Good idea, the function will be documented in subsequent commits.

It has no equivelant in OpenCL backend because it isn't required by any OpenCL driven projects. Is there a way you would like this to be marked as CUDA specific?

Copy link
Contributor

Choose a reason for hiding this comment

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

I think using any symbols from sycl::detail namespace is dangerous as it's by design intended for internal implementation details.
I suggest oneMKL to use "public/standard/stable" API if possible.

tagging @mkrainiuk, @mehdi-goli.

Copy link
Contributor

Choose a reason for hiding this comment

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

This is meant to be a temporary fix until there is a SYCL extension to cover for this functionality, that's why its exposing some implementation details, because there is no public API for this at this point.

Copy link
Contributor

Choose a reason for hiding this comment

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

Is there a SYCL extension in flight to support this?

What's exactly the functionality achieved here (it's hard to tell for sure because there is not documentation of this extension)?

I'd like to approve this to unblock MKL, but please create an issue (or just PR) to document the piextContextSetExtendedDeleter and also to discuss if there is a better way to achieve what's needed.

Copy link
Contributor

@smaslov-intel smaslov-intel left a comment

Choose a reason for hiding this comment

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

Approved, if agreed on a follow up issue/PR to clarify the extension.

@bader bader merged commit a69cdda into intel:sycl Apr 20, 2020
alexbatashev pushed a commit to alexbatashev/llvm that referenced this pull request Apr 21, 2020
…c_abi_checks

* origin/sycl:
  [SYCL][Driver] Enforce unique filenames when -save-temps is used (intel#1545)
  [SYCL] [xmethods] Allow replacing xmethod script (intel#1532)
  [SYCL] Add tests for inline asm feature (intel#1444)
  [SYCL][Doc] Add device_specific_kernel_queries extension. (intel#1540)
  [SYCL][USM] Remove unused header and unnecessary includes (intel#1537)
  Fix check-llvm dependencies (intel#1547)
  [SYCL] Add __SYCL_EXPORT to declaration of contextSetExtendedDeleter (intel#1531)
  [SYCL][Doc] Add static local memory query extension. (intel#1539)
  [SYCL][Doc] Add sycl_bitcast extension (intel#1541)
  [SYCL][NFC] Temporarily disable sporadically failing test (intel#1533)
  [SYCL][NFC] Adjust codeowners for sycl directory (intel#1529)
  [SYCL] Fix processing of spec consts referenced twice (intel#1524)
  [SYCL] Use correct macro name in export.hpp (intel#1527)
  [Driver][NFC] Fix -help information for -Xs options (intel#1530)
  [SYCL][Doc] Add Graph Scheduler design documentation (intel#1457)
  [SYCL] Add diagnostics for long double in device code (intel#1512)
  [SYCL] Add a mutex to state-modifying program functions (intel#1204)
  [SYCL][Test] Add Devicelib tests (intel#1256)
  [SYCL] Refactor semantic checks for variable types (intel#1513)
@keryell
Copy link
Contributor

keryell commented Apr 22, 2020

I have the feeling it is related to internal Khronos discussion https://gitlab.khronos.org/sycl/Specification/issues/289

@smaslov-intel
Copy link
Contributor

@StuartDAdams , please create an issue (or PR) with the definition of the piextContextSetExtendedDeleter

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.

6 participants