AI/rocm-systems
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity

rocr: Add thread priority for AsyncEventHandler

Browse Source 
Set priority to maximum for signal event handler and minimum for
exceptions event handler.

Change-Id: I1b982d3c2e4c880fafc073fe1a542d01692a6fdc


[ROCm/ROCR-Runtime commit: 7ea25ebb85]
This commit is contained in:
David Yat Sin
2024-10-02 16:28:06 +00:00
parent 15cc61baf4
commit 922b61ddee
5 changed files with 71 additions and 7 deletions
Download Patch File Download Diff File Expand all files Collapse all files
projects/rocr-runtime/runtime/hsa-runtime/core/runtime/runtime.cpp
+5 -2
View File
@@ -809,14 +809,17 @@ hsa_status_t Runtime::SetAsyncSignalHandler(hsa_signal_t signal,
void* arg) {
struct AsyncEventsInfo* asyncInfo = &asyncSignals_;
int priority = runtime_singleton_->flag().async_events_thread_priority();
if (signal.handle != 0) {
// Indicate that this signal is in use.
hsa_signal_handle(signal)->Retain();
core::Signal* coreSignal = core::Signal::Convert(signal);
if (coreSignal->EopEvent() && coreSignal->EopEvent()->EventData.EventType != HSA_EVENTTYPE_SIGNAL)
if (coreSignal->EopEvent() && coreSignal->EopEvent()->EventData.EventType != HSA_EVENTTYPE_SIGNAL) {
priority = os::OS_THREAD_PRIORITY_DEFAULT;
asyncInfo = &asyncExceptions_;
}
}
ScopedAcquire<HybridMutex> scope_lock(&asyncInfo->control.lock);
@@ -835,7 +838,7 @@ hsa_status_t Runtime::SetAsyncSignalHandler(hsa_signal_t signal,
// Start event monitoring thread
asyncInfo->control.exit = false;
asyncInfo->control.async_events_thread_ =
os::CreateThread(AsyncEventsLoop, asyncInfo);
os::CreateThread(AsyncEventsLoop, asyncInfo, 0, priority);
if (asyncInfo->control.async_events_thread_ == NULL) {
assert(false && "Asyncronous events thread creation error.");
return HSA_STATUS_ERROR_OUT_OF_RESOURCES;