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 D | hsa.h | 172 } 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 D | rtl.cpp | 50 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()
|