Home
last modified time | relevance | path

Searched refs:hsa_queue_t (Results 1 – 2 of 2) sorted by relevance

/llvm-project-15.0.7/openmp/libomptarget/plugins/amdgpu/dynamic_hsa/
H A Dhsa.h172 } hsa_queue_t; typedef
177 hsa_queue_t *source, void *data),
179 uint32_t group_segment_size, hsa_queue_t **queue);
181 hsa_status_t hsa_queue_destroy(hsa_queue_t *queue);
183 uint64_t hsa_queue_load_read_index_scacquire(const hsa_queue_t *queue);
185 uint64_t hsa_queue_add_write_index_relaxed(const hsa_queue_t *queue,
/llvm-project-15.0.7/openmp/libomptarget/plugins/amdgpu/src/
H A Drtl.cpp50 uint64_t hostrpc_assign_buffer(hsa_agent_t Agent, hsa_queue_t *ThisQ,
59 __attribute__((weak)) uint64_t hostrpc_assign_buffer(hsa_agent_t, hsa_queue_t *, in hostrpc_assign_buffer() argument
273 static void callbackQueue(hsa_status_t Status, hsa_queue_t *Source, in callbackQueue()
399 hsa_queue_t *Q = nullptr; in createQueues()
423 hsa_queue_t *next() { in next()
431 hsa_queue_t *HSAQueues[NUM_QUEUES_PER_DEVICE] = {};
440 void operator()(hsa_queue_t *Q) { in operator ()()
1350 static uint64_t acquireAvailablePacketId(hsa_queue_t *Queue) { in acquireAvailablePacketId()
1431 hsa_queue_t *Queue = DeviceInfo().HSAQueueSchedulers[DeviceId].next(); in runRegionLocked()