dist/include/hsa.h

38 typedef struct hsa_signal_s { uint64_t handle; } hsa_signal_t;
130   hsa_signal_t doorbell_signal;
151   hsa_signal_t completion_signal;
237   hsa_signal_t dep_signal[5];
239   hsa_signal_t completion_signal;
316   hsa_signal_t completion_signal;
386   hsa_signal_t dep_signal[5];
388   hsa_signal_t completion_signal;
408 void hsa_signal_add_acq_rel(hsa_signal_t signal, hsa_signal_value_t value);
410 void hsa_signal_add_acquire(hsa_signal_t signal, hsa_signal_value_t value);
412 void hsa_signal_add_relaxed(hsa_signal_t signal, hsa_signal_value_t value);
414 void hsa_signal_add_release(hsa_signal_t signal, hsa_signal_value_t value);
423 hsa_signal_value_t hsa_signal_load_acquire(hsa_signal_t signal);
425 hsa_signal_value_t hsa_signal_load_relaxed(hsa_signal_t signal);
432 void hsa_signal_subtract_acq_rel(hsa_signal_t signal, hsa_signal_value_t value);
434 void hsa_signal_subtract_acquire(hsa_signal_t signal, hsa_signal_value_t value);
436 void hsa_signal_subtract_relaxed(hsa_signal_t signal, hsa_signal_value_t value);
438 void hsa_signal_subtract_release(hsa_signal_t signal, hsa_signal_value_t value);
443 void hsa_signal_xor_acq_rel(hsa_signal_t signal, hsa_signal_value_t value);
445 void hsa_signal_xor_acquire(hsa_signal_t signal, hsa_signal_value_t value);
447 void hsa_signal_xor_relaxed(hsa_signal_t signal, hsa_signal_value_t value);
449 void hsa_signal_xor_release(hsa_signal_t signal, hsa_signal_value_t value);
461 void hsa_signal_store_relaxed(hsa_signal_t signal, hsa_signal_value_t value);
463 void hsa_signal_store_release(hsa_signal_t signal, hsa_signal_value_t value);
464 hsa_status_t hsa_signal_destroy(hsa_signal_t signal);
497 hsa_signal_value_t hsa_signal_wait_acquire(hsa_signal_t signal,
503 hsa_signal_value_t hsa_signal_wait_relaxed(hsa_signal_t signal,
517                                hsa_signal_t *signal);
521 hsa_signal_value_t hsa_signal_cas_acq_rel(hsa_signal_t signal,
525 hsa_signal_value_t hsa_signal_cas_acquire(hsa_signal_t signal,
529 hsa_signal_value_t hsa_signal_cas_relaxed(hsa_signal_t signal,
533 hsa_signal_value_t hsa_signal_cas_release(hsa_signal_t signal,
566 void hsa_signal_and_acq_rel(hsa_signal_t signal, hsa_signal_value_t value);
568 void hsa_signal_and_acquire(hsa_signal_t signal, hsa_signal_value_t value);
570 void hsa_signal_and_relaxed(hsa_signal_t signal, hsa_signal_value_t value);
572 void hsa_signal_and_release(hsa_signal_t signal, hsa_signal_value_t value);
587 void hsa_signal_or_acq_rel(hsa_signal_t signal, hsa_signal_value_t value);
589 void hsa_signal_or_acquire(hsa_signal_t signal, hsa_signal_value_t value);
591 void hsa_signal_or_relaxed(hsa_signal_t signal, hsa_signal_value_t value);
593 void hsa_signal_or_release(hsa_signal_t signal, hsa_signal_value_t value);
596                                    hsa_signal_t doorbell_signal,
615 hsa_signal_value_t hsa_signal_exchange_acq_rel(hsa_signal_t signal,
618 hsa_signal_value_t hsa_signal_exchange_acquire(hsa_signal_t signal,
621 hsa_signal_value_t hsa_signal_exchange_relaxed(hsa_signal_t signal,
624 hsa_signal_value_t hsa_signal_exchange_release(hsa_signal_t signal,