dist/include/hsa.h

343 typedef int64_t hsa_signal_value_t;
345 typedef int32_t hsa_signal_value_t;
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);
497 hsa_signal_value_t hsa_signal_wait_acquire(hsa_signal_t signal,
499                                            hsa_signal_value_t compare_value,
503 hsa_signal_value_t hsa_signal_wait_relaxed(hsa_signal_t signal,
505                                            hsa_signal_value_t compare_value,
514 hsa_status_t hsa_signal_create(hsa_signal_value_t initial_value,
521 hsa_signal_value_t hsa_signal_cas_acq_rel(hsa_signal_t signal,
522                                           hsa_signal_value_t expected,
523                                           hsa_signal_value_t value);
525 hsa_signal_value_t hsa_signal_cas_acquire(hsa_signal_t signal,
526                                           hsa_signal_value_t expected,
527                                           hsa_signal_value_t value);
529 hsa_signal_value_t hsa_signal_cas_relaxed(hsa_signal_t signal,
530                                           hsa_signal_value_t expected,
531                                           hsa_signal_value_t value);
533 hsa_signal_value_t hsa_signal_cas_release(hsa_signal_t signal,
534                                           hsa_signal_value_t expected,
535                                           hsa_signal_value_t value);
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);
615 hsa_signal_value_t hsa_signal_exchange_acq_rel(hsa_signal_t signal,
616                                                hsa_signal_value_t value);
618 hsa_signal_value_t hsa_signal_exchange_acquire(hsa_signal_t signal,
619                                                hsa_signal_value_t value);
621 hsa_signal_value_t hsa_signal_exchange_relaxed(hsa_signal_t signal,
622                                                hsa_signal_value_t value);
624 hsa_signal_value_t hsa_signal_exchange_release(hsa_signal_t signal,
625                                                hsa_signal_value_t value);