diff options
| author | JRPan <[email protected]> | 2025-08-18 23:09:47 -0700 |
|---|---|---|
| committer | GitHub <[email protected]> | 2025-08-19 06:09:47 +0000 |
| commit | 21b18be3832b80b00d4890f041818bac431866e7 (patch) | |
| tree | 4a8801a93a6dde20b747ef6db509215894c9f3ec /src/gpgpusim_entrypoint.cc | |
| parent | 33644740f15e0fa9f3d64ff98956569b2acf47bc (diff) | |
running formatter (#126)
* running formatter
* consolidate CI runs
* use cluster to run formatter
* use cluster to run formatter
* Add a CI-Success step
Diffstat (limited to 'src/gpgpusim_entrypoint.cc')
| -rw-r--r-- | src/gpgpusim_entrypoint.cc | 20 |
1 files changed, 12 insertions, 8 deletions
diff --git a/src/gpgpusim_entrypoint.cc b/src/gpgpusim_entrypoint.cc index be49229..4462dc3 100644 --- a/src/gpgpusim_entrypoint.cc +++ b/src/gpgpusim_entrypoint.cc @@ -58,7 +58,8 @@ class stream_manager *g_stream_manager() { extern void SST_callback_cudaThreadSynchronize_done(); extern void SST_callback_cudaStreamSynchronize_done(cudaStream_t stream); __attribute__((weak)) void SST_callback_cudaThreadSynchronize_done() {} -__attribute__((weak)) void SST_callback_cudaStreamSynchronize_done(cudaStream_t stream) {} +__attribute__((weak)) void SST_callback_cudaStreamSynchronize_done( + cudaStream_t stream) {} void *gpgpu_sim_thread_sequential(void *ctx_ptr) { gpgpu_context *ctx = (gpgpu_context *)ctx_ptr; @@ -102,7 +103,8 @@ void *gpgpu_sim_thread_concurrent(void *ctx_ptr) { fflush(stdout); } while (ctx->the_gpgpusim->g_stream_manager->empty_protected() && - !ctx->the_gpgpusim->g_sim_done); + !ctx->the_gpgpusim->g_sim_done) + ; if (g_debug_execution >= 3) { printf("GPGPU-Sim: ** START simulation thread (detected work) **\n"); ctx->the_gpgpusim->g_stream_manager->print(stdout); @@ -191,7 +193,8 @@ bool SST_Cycle() { // Check if Synchronize is done when SST previously requested // cudaThreadSynchronize if (GPGPU_Context()->requested_synchronize && - ((g_stream_manager()->empty_protected() && !GPGPUsim_ctx_ptr()->g_sim_active) || + ((g_stream_manager()->empty_protected() && + !GPGPUsim_ctx_ptr()->g_sim_active) || GPGPUsim_ctx_ptr()->g_sim_done)) { SST_callback_cudaThreadSynchronize_done(); GPGPU_Context()->requested_synchronize = false; @@ -199,19 +202,20 @@ bool SST_Cycle() { // Polling to check for each stream if it is marked for requested with sync if (g_stream_manager()->get_stream_zero()->requested_synchronize() && - ((g_stream_manager()->empty_protected() && !GPGPUsim_ctx_ptr()->g_sim_active) || - GPGPUsim_ctx_ptr()->g_sim_done)) { + ((g_stream_manager()->empty_protected() && + !GPGPUsim_ctx_ptr()->g_sim_active) || + GPGPUsim_ctx_ptr()->g_sim_done)) { SST_callback_cudaStreamSynchronize_done(0); g_stream_manager()->get_stream_zero()->reset_request_synchronize(); } // Iterate through each stream to check if SST is waiting on // it and it does not have any operation - std::list<CUstream_st *>& streams = g_stream_manager()->get_concurrent_streams(); + std::list<CUstream_st *> &streams = + g_stream_manager()->get_concurrent_streams(); for (auto it = streams.begin(); it != streams.end(); it++) { CUstream_st *stream = *it; - if (stream->requested_synchronize() && - stream->empty()) { + if (stream->requested_synchronize() && stream->empty()) { // This stream is ready SST_callback_cudaStreamSynchronize_done(stream); stream->reset_request_synchronize(); |
