oneapi-src / oneapi-src/level-zero

[Feature Request] Add equivalent of cudaDeviceSynchronize()

Open
#118 3 comments 1 reaction 0 assignees View on GitHub

Nobody has claimed this yet.

Dominant language
C++
Stars
335
Forks
140
Avg merge
12h 32m
Merged PRs (30d)
5

Description

Many applications written in CUDA rely on the whole device synchronization behavior of cudaDeviceSynchronize().
Trying to migrate applications that use this to SYCL, for example, is not really possible.

Question: Why does this need to be in L0? Why can't you solve it at a higher level?
Answer: The higher level layer may not have 100% visibility over how level zero is being used. If the L0 plugin in DPC++ tried to add something like this - programs may have incorrect behavior if the user application ALSO uses L0 directly - the plugin has no knowledge of any queues created in the user application or libaries.

Contributor guide

Open the contributing guide

First steps

  1. Read the whole issue, then the project's contributing guide.
  2. Comment on the issue to say you are picking it up — it saves two people doing the same work.
  3. Fork the repository and make your change on a branch.
  4. Open a pull request that references the issue number.

Research direction

Start by comparing the requested cudaDeviceSynchronize() behavior with the synchronization capabilities described by the Level Zero specification headers and loader. Define the required whole-device semantics and determine which Level Zero API surface would own them; the issue is done only when the behavior and design are specified clearly enough for implementation.

Written by the indexing model from the issue text.

Assessment

Tech stack
cpp
Domain
api
Issue type
Feature
Difficulty
5/5
Estimated time
Over a week
Activity status
Stale
Clarity
Needs clarification
Newbie friendliness
25/100

Get new issues in your inbox

A short digest of beginner-friendly GitHub issues.