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, pi_uint32 stream_token=std::numeric_limits< pi_uint32 >::max()) |
static pi_event | make_with_native (pi_context context, CUevent eventNative) |
static pi_event | make_native (pi_command_type type, pi_queue queue, hipStream_t stream, pi_uint32 stream_token=std::numeric_limits< pi_uint32 >::max()) |
Public Attributes | |
cm_support::CmEvent * | CmEventPtr = nullptr |
cm_support::CmQueue * | OwnerQueue = nullptr |
pi_context | Context = nullptr |
bool | IsDummyEvent = false |
PI Event mapping to CUevent.
PI Event mapping to hipEvent_t.
Definition at line 633 of file pi_cuda.hpp.
using _pi_event::native_type = hipEvent_t |
Definition at line 614 of file pi_hip.hpp.
using _pi_event::native_type = CUevent |
Definition at line 635 of file pi_cuda.hpp.
_pi_event::~_pi_event | ( | ) |
Definition at line 638 of file pi_cuda.cpp.
References cuda_piContextRelease(), and cuda_piQueueRelease().
|
inline |
Definition at line 202 of file pi_esimd_emulator.hpp.
Referenced by make_native(), and make_with_native().
_pi_event::~_pi_event | ( | ) |
|
inlinenoexcept |
Definition at line 681 of file pi_cuda.hpp.
Referenced by release().
|
inline |
Definition at line 656 of file pi_hip.hpp.
|
inline |
Definition at line 677 of file pi_cuda.hpp.
|
inlinenoexcept |
Definition at line 622 of file pi_hip.hpp.
|
inlinenoexcept |
Definition at line 643 of file pi_cuda.hpp.
|
inlinenoexcept |
Definition at line 630 of file pi_hip.hpp.
|
inlinenoexcept |
Definition at line 651 of file pi_cuda.hpp.
|
inlinenoexcept |
Definition at line 628 of file pi_hip.hpp.
|
inlinenoexcept |
Definition at line 649 of file pi_cuda.hpp.
Referenced by _pi_queue::get_next_compute_stream().
|
inlinenoexcept |
Definition at line 652 of file pi_hip.hpp.
|
inlinenoexcept |
Definition at line 673 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 698 of file pi_cuda.cpp.
References _pi_queue::get_device(), _pi_device::get_elapsed_time(), is_recorded(), and is_started().
|
inlinenoexcept |
Definition at line 658 of file pi_hip.hpp.
|
inlinenoexcept |
Definition at line 679 of file pi_cuda.hpp.
|
inlinenoexcept |
Definition at line 640 of file pi_hip.hpp.
References is_completed(), is_recorded(), PI_EVENT_COMPLETE, PI_EVENT_RUNNING, and PI_EVENT_SUBMITTED.
|
inlinenoexcept |
Definition at line 661 of file pi_cuda.hpp.
References is_completed(), is_recorded(), PI_EVENT_COMPLETE, PI_EVENT_RUNNING, and PI_EVENT_SUBMITTED.
|
inlinenoexcept |
Definition at line 624 of file pi_hip.hpp.
|
inlinenoexcept |
Definition at line 645 of file pi_cuda.hpp.
pi_uint64 _pi_event::get_queued_time | ( | ) | const |
pi_uint64 _pi_event::get_queued_time | ( | ) | const |
Definition at line 688 of file pi_cuda.cpp.
References _pi_queue::get_device(), _pi_device::get_elapsed_time(), and is_started().
|
inlinenoexcept |
Definition at line 632 of file pi_hip.hpp.
|
inlinenoexcept |
Definition at line 653 of file pi_cuda.hpp.
pi_uint64 _pi_event::get_start_time | ( | ) | const |
pi_uint64 _pi_event::get_start_time | ( | ) | const |
Definition at line 693 of file pi_cuda.cpp.
References _pi_queue::get_device(), _pi_device::get_elapsed_time(), and is_started().
|
inlinenoexcept |
Definition at line 626 of file pi_hip.hpp.
|
inlinenoexcept |
Definition at line 647 of file pi_cuda.hpp.
Referenced by _pi_queue::get_next_compute_stream().
|
inline |
Definition at line 654 of file pi_hip.hpp.
|
inline |
Definition at line 675 of file pi_cuda.hpp.
|
noexcept |
|
noexcept |
Definition at line 663 of file pi_cuda.cpp.
Referenced by get_execution_status().
|
inlinenoexcept |
Definition at line 634 of file pi_hip.hpp.
|
inlinenoexcept |
Definition at line 655 of file pi_cuda.hpp.
Referenced by get_end_time(), get_execution_status(), and record().
|
inlinenoexcept |
Definition at line 636 of file pi_hip.hpp.
|
inlinenoexcept |
Definition at line 657 of file pi_cuda.hpp.
Referenced by get_end_time(), get_queued_time(), get_start_time(), record(), and start().
|
inlinestatic |
Definition at line 697 of file pi_cuda.hpp.
References _pi_event(), and _pi_queue::get_context().
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_piextUSMEnqueueMemcpy2D(), 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_piextUSMEnqueueMemcpy2D(), hip_piextUSMEnqueueMemset(), and hip_piextUSMEnqueuePrefetch().
|
inlinestatic |
Definition at line 674 of file pi_hip.hpp.
References _pi_event(), and _pi_queue::get_context().
|
inlinestatic |
Definition at line 703 of file pi_cuda.hpp.
References _pi_event().
Referenced by cuda_piextEventCreateWithNativeHandle().
pi_result _pi_event::record | ( | ) |
pi_result _pi_event::record | ( | ) |
Definition at line 703 of file pi_cuda.cpp.
References sycl::_V1::detail::pi::die(), _pi_queue::get_next_event_id(), is_recorded(), and is_started().
pi_result _pi_event::release | ( | ) |
pi_result _pi_event::release | ( | ) |
Definition at line 745 of file pi_cuda.cpp.
References backend_has_ownership(), PI_QUEUE_FLAG_PROFILING_ENABLE, 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 645 of file pi_cuda.cpp.
References is_started(), PI_QUEUE_FLAG_PROFILING_ENABLE, and _pi_queue::properties_.
pi_result _pi_event::wait | ( | ) |
pi_result _pi_event::wait | ( | ) |
Definition at line 733 of file pi_cuda.cpp.
cm_support::CmEvent* _pi_event::CmEventPtr = nullptr |
Definition at line 204 of file pi_esimd_emulator.hpp.
Referenced by piEventGetInfo(), piEventRelease(), and piEventsWait().
pi_context _pi_event::Context = nullptr |
Definition at line 206 of file pi_esimd_emulator.hpp.
bool _pi_event::IsDummyEvent = false |
Definition at line 207 of file pi_esimd_emulator.hpp.
Referenced by piEventGetInfo(), and piEventRelease().
cm_support::CmQueue* _pi_event::OwnerQueue = nullptr |
Definition at line 205 of file pi_esimd_emulator.hpp.
Referenced by piEventRelease().