PI Event mapping to CUevent. More...
#include <cuda/pi_cuda.hpp>
Public Types | |
using | native_type = CUevent |
using | native_type = hipEvent_t |
Static Public Member Functions | |
static pi_event | make_native (pi_command_type type, pi_queue queue, CUstream stream) |
static pi_event | make_native (pi_command_type type, pi_queue queue) |
Public Attributes | |
cm_support::CmEvent * | CmEventPtr = nullptr |
cm_support::CmQueue * | OwnerQueue = nullptr |
pi_context | Context = nullptr |
bool | IsDummyEvent = false |
ze_event_handle_t | ZeEvent |
bool | OwnZeEvent |
ze_event_pool_handle_t | ZeEventPool |
pi_event | HostVisibleEvent = {nullptr} |
ze_command_list_handle_t | ZeCommandList |
pi_queue | Queue = {nullptr} |
pi_command_type | CommandType |
void * | CommandData |
_pi_ze_event_list_t | WaitList |
bool | CleanedUp = {false} |
bool | Completed = {false} |
PI Event mapping to CUevent.
PI Event mapping to hipEvent_t.
Definition at line 460 of file pi_cuda.hpp.
using _pi_event::native_type = hipEvent_t |
Definition at line 406 of file pi_hip.hpp.
using _pi_event::native_type = CUevent |
Definition at line 462 of file pi_cuda.hpp.
_pi_event::~_pi_event | ( | ) |
Definition at line 423 of file pi_cuda.cpp.
References cuda_piContextRelease(), and cuda_piQueueRelease().
|
inline |
Definition at line 194 of file pi_esimd_emulator.hpp.
Referenced by make_native().
_pi_event::~_pi_event | ( | ) |
|
inline |
Definition at line 1194 of file pi_level_zero.hpp.
Definition at line 5419 of file pi_level_zero.cpp.
References _pi_ze_event_list_t::collectEventsForReleaseAndDestroyPiZeEventList(), CommandData, CommandType, cl::sycl::detail::pi::die(), EventRelease(), PI_CALL, PI_COMMAND_TYPE_MEM_BUFFER_COPY, PI_COMMAND_TYPE_NDRANGE_KERNEL, PI_SUCCESS, piKernelRelease(), Queue, WaitList, and ZE_CALL_NOCHECK.
Referenced by EventRelease(), piEventsWait(), and _pi_queue::synchronize().
|
inline |
Definition at line 444 of file pi_hip.hpp.
|
inline |
Definition at line 502 of file pi_cuda.hpp.
|
inlinenoexcept |
Definition at line 414 of file pi_hip.hpp.
|
inlinenoexcept |
Definition at line 470 of file pi_cuda.hpp.
Referenced by cl::sycl::detail::Command::waitForEvents().
|
inlinenoexcept |
Definition at line 418 of file pi_hip.hpp.
|
inlinenoexcept |
Definition at line 476 of file pi_cuda.hpp.
|
inlinenoexcept |
Definition at line 440 of file pi_hip.hpp.
|
inlinenoexcept |
Definition at line 498 of file pi_cuda.hpp.
Referenced by cuda_piEventsWait(), and hip_piEventsWait().
pi_uint64 _pi_event::get_end_time | ( | ) | const |
pi_uint64 _pi_event::get_end_time | ( | ) | const |
Definition at line 483 of file pi_cuda.cpp.
References _pi_platform::evBase_, is_recorded(), and is_started().
|
inlinenoexcept |
Definition at line 446 of file pi_hip.hpp.
|
inlinenoexcept |
Definition at line 504 of file pi_cuda.hpp.
|
inlinenoexcept |
Definition at line 428 of file pi_hip.hpp.
References is_completed(), is_recorded(), PI_EVENT_COMPLETE, PI_EVENT_RUNNING, and PI_EVENT_SUBMITTED.
|
inlinenoexcept |
Definition at line 486 of file pi_cuda.hpp.
References is_completed(), is_recorded(), PI_EVENT_COMPLETE, PI_EVENT_RUNNING, and PI_EVENT_SUBMITTED.
|
inlinenoexcept |
Definition at line 416 of file pi_hip.hpp.
|
inlinenoexcept |
Definition at line 472 of file pi_cuda.hpp.
pi_uint64 _pi_event::get_queued_time | ( | ) | const |
pi_uint64 _pi_event::get_queued_time | ( | ) | const |
Definition at line 465 of file pi_cuda.cpp.
References _pi_platform::evBase_, and is_started().
|
inlinenoexcept |
Definition at line 420 of file pi_hip.hpp.
|
inlinenoexcept |
Definition at line 478 of file pi_cuda.hpp.
pi_uint64 _pi_event::get_start_time | ( | ) | const |
pi_uint64 _pi_event::get_start_time | ( | ) | const |
Definition at line 474 of file pi_cuda.cpp.
References _pi_platform::evBase_, and is_started().
|
inlinenoexcept |
Definition at line 474 of file pi_cuda.hpp.
pi_result _pi_event::getOrCreateHostVisibleEvent | ( | ze_event_handle_t & | HostVisibleEvent | ) |
Definition at line 5188 of file pi_level_zero.cpp.
References createEventAndAssociateQueue(), cl::sycl::detail::pi::die(), PI_COMMAND_TYPE_USER, PI_SUCCESS, and ZE_CALL.
|
inline |
Definition at line 442 of file pi_hip.hpp.
|
inline |
Definition at line 500 of file pi_cuda.hpp.
|
noexcept |
|
noexcept |
Definition at line 448 of file pi_cuda.cpp.
Referenced by get_execution_status().
|
inlinenoexcept |
Definition at line 422 of file pi_hip.hpp.
|
inlinenoexcept |
Definition at line 480 of file pi_cuda.hpp.
Referenced by get_end_time(), get_execution_status(), and record().
|
inlinenoexcept |
Definition at line 424 of file pi_hip.hpp.
|
inlinenoexcept |
Definition at line 482 of file pi_cuda.hpp.
Referenced by get_end_time(), get_queued_time(), get_start_time(), record(), and start().
|
inline |
Definition at line 1221 of file pi_level_zero.hpp.
Referenced by _pi_context::decrementUnreleasedEventsInPool().
|
inline |
Definition at line 1227 of file pi_level_zero.hpp.
References PI_QUEUE_PROFILING_ENABLE.
Referenced by _pi_context::decrementUnreleasedEventsInPool().
|
inlinestatic |
Definition at line 461 of file pi_hip.hpp.
References _pi_event().
|
inlinestatic |
Definition at line 519 of file pi_cuda.hpp.
References _pi_event().
Referenced by cuda_piEnqueueEventsWaitWithBarrier(), cuda_piEnqueueKernelLaunch(), cuda_piEnqueueMemBufferCopy(), cuda_piEnqueueMemBufferCopyRect(), cuda_piEnqueueMemBufferFill(), cuda_piEnqueueMemBufferMap(), cuda_piEnqueueMemBufferRead(), cuda_piEnqueueMemBufferReadRect(), cuda_piEnqueueMemBufferWrite(), cuda_piEnqueueMemBufferWriteRect(), cuda_piEnqueueMemImageCopy(), cuda_piEnqueueMemImageRead(), cuda_piEnqueueMemImageWrite(), cuda_piEnqueueMemUnmap(), cuda_piextUSMEnqueueMemAdvise(), cuda_piextUSMEnqueueMemcpy(), cuda_piextUSMEnqueueMemset(), cuda_piextUSMEnqueuePrefetch(), hip_piEnqueueEventsWaitWithBarrier(), hip_piEnqueueKernelLaunch(), hip_piEnqueueMemBufferCopy(), hip_piEnqueueMemBufferCopyRect(), hip_piEnqueueMemBufferFill(), hip_piEnqueueMemBufferMap(), hip_piEnqueueMemBufferRead(), hip_piEnqueueMemBufferReadRect(), hip_piEnqueueMemBufferWrite(), hip_piEnqueueMemBufferWriteRect(), hip_piEnqueueMemImageCopy(), hip_piEnqueueMemImageRead(), hip_piEnqueueMemImageWrite(), hip_piEnqueueMemUnmap(), hip_piextUSMEnqueueMemcpy(), hip_piextUSMEnqueueMemset(), and hip_piextUSMEnqueuePrefetch().
pi_result _pi_event::record | ( | ) |
pi_result _pi_event::record | ( | ) |
Definition at line 492 of file pi_cuda.cpp.
References cl::sycl::detail::pi::die(), _pi_queue::get_next_event_id(), is_recorded(), is_started(), PI_INVALID_EVENT, PI_INVALID_OPERATION, PI_INVALID_QUEUE, and PI_SUCCESS.
pi_result _pi_event::release | ( | ) |
pi_result _pi_event::release | ( | ) |
Definition at line 534 of file pi_cuda.cpp.
References PI_QUEUE_PROFILING_ENABLE, PI_SUCCESS, and _pi_queue::properties_.
Referenced by piEnqueueKernelLaunch(), piEnqueueMemBufferMap(), piEnqueueMemBufferRead(), piEnqueueMemImageRead(), and piEnqueueMemUnmap().
pi_result _pi_event::start | ( | ) |
pi_result _pi_event::start | ( | ) |
Definition at line 430 of file pi_cuda.cpp.
References is_started(), PI_QUEUE_PROFILING_ENABLE, PI_SUCCESS, and _pi_queue::properties_.
pi_result _pi_event::wait | ( | ) |
pi_result _pi_event::wait | ( | ) |
Definition at line 522 of file pi_cuda.cpp.
bool _pi_event::CleanedUp = {false} |
Definition at line 1261 of file pi_level_zero.hpp.
Referenced by EventRelease(), _pi_queue::executeCommandList(), and piextEventCreateWithNativeHandle().
cm_support::CmEvent* _pi_event::CmEventPtr = nullptr |
Definition at line 196 of file pi_esimd_emulator.hpp.
Referenced by piEventRelease(), and piEventsWait().
void* _pi_event::CommandData |
Definition at line 1247 of file pi_level_zero.hpp.
Referenced by cleanup(), and EventRelease().
pi_command_type _pi_event::CommandType |
Definition at line 1240 of file pi_level_zero.hpp.
Referenced by cleanup(), EventRelease(), and piEventGetInfo().
bool _pi_event::Completed = {false} |
Definition at line 1267 of file pi_level_zero.hpp.
Referenced by piEventGetInfo(), and _pi_queue::synchronize().
pi_context _pi_event::Context = nullptr |
Definition at line 198 of file pi_esimd_emulator.hpp.
Referenced by EventRelease(), piEventGetInfo(), and piEventGetProfilingInfo().
pi_event _pi_event::HostVisibleEvent = {nullptr} |
Definition at line 1220 of file pi_level_zero.hpp.
Referenced by _pi_ze_event_list_t::createAndRetainPiZeEventList(), EventRelease(), piEventGetInfo(), and piEventsWait().
bool _pi_event::IsDummyEvent = false |
Definition at line 199 of file pi_esimd_emulator.hpp.
Referenced by piEventRelease().
cm_support::CmQueue* _pi_event::OwnerQueue = nullptr |
Definition at line 197 of file pi_esimd_emulator.hpp.
Referenced by piEventRelease().
bool _pi_event::OwnZeEvent |
Definition at line 1205 of file pi_level_zero.hpp.
Referenced by EventRelease().
pi_queue _pi_event::Queue = {nullptr} |
Definition at line 1239 of file pi_level_zero.hpp.
Referenced by cleanup(), _pi_ze_event_list_t::createAndRetainPiZeEventList(), EventRelease(), piEventGetInfo(), piEventGetProfilingInfo(), piEventsWait(), and piextEventGetNativeHandle().
_pi_ze_event_list_t _pi_event::WaitList |
Definition at line 1253 of file pi_level_zero.hpp.
Referenced by cleanup().
ze_command_list_handle_t _pi_event::ZeCommandList |
Definition at line 1235 of file pi_level_zero.hpp.
Referenced by _pi_queue::executeOpenCommandListWithEvent(), and _pi_queue::synchronize().
ze_event_handle_t _pi_event::ZeEvent |
Definition at line 1201 of file pi_level_zero.hpp.
Referenced by _pi_ze_event_list_t::createAndRetainPiZeEventList(), EventRelease(), _pi_queue::executeCommandList(), piEventGetProfilingInfo(), piextEventGetNativeHandle(), and _pi_queue::synchronize().
ze_event_pool_handle_t _pi_event::ZeEventPool |
Definition at line 1208 of file pi_level_zero.hpp.
Referenced by _pi_context::decrementUnreleasedEventsInPool().