Zac*_*ack 2 c multithreading openmp race-condition
我的程序中有以下代码,我想使用 OpenMP 加速它。
...
for(i=curr_index; i < curr_index + rx_size; i+=2){
int64_t tgt = rcvq[i];
int64_t src = rcvq[i+1];
if (!TEST(tgt)) {
pred[tgt] = src;
newq[newq_count++] = tgt;
}
}
Run Code Online (Sandbox Code Playgroud)
目前,我有一个版本如下:
...
chunk = rx_sz / omp_nthreads;
#pragma omp parallel for num_threads(omp_nthreads)
for (ii = 0; ii < omp_nthreads; ii++) {
int start = curr_index + ii * chunk;
for (index = start; index < start + chunk; index +=2) {
int64_t tgt = rcvq[index];
int64_t src = rcvq[index+1];
if (!TEST(tgt)) {
pred[tgt] = src;
#pragma omp critical
newq[newq_count++] = tgt;
}
}
}
Run Code Online (Sandbox Code Playgroud)
当我运行 OpenMP 版本时,我发现与原始版本相比性能大幅下降。我认为这个问题可能是因为“omp critical”阻止了并行处理。我想知道我的代码可以增强哪些功能,以便我可以获得比串行版本更好的性能。在代码中,rx_sz始终是omp_nthreads的倍数。
是的,关键部分限制了你的表现。您应该在本地收集每个线程的结果,然后合并它们。
size_t newq_offset = 0;
#pragma omp parallel
{
// Figure out something clever here...
const size_t max_newq_per_thread = max_newq / omp_get_num_threads();
int64_t* local_newq = malloc(max_results_per_thread * sizeof(int64_t));
size_t local_newq_count = 0;
#pragma omp parallel for
for (i=curr_index; i < curr_index + rx_size; i+=2)
int64_t tgt = rcvq[2*index];
int64_t src = rcvq[2*index+1];
if (!TEST(tgt)) {
pred[tgt] = src;
local_newq_count++;
assert(local_newq_count < max_newq_per_thread);
local_newq[local_newq_count] = tgt;
}
}
int local_offset;
#pragma omp atomic capture
{
local_offset = offset;
offset += local_newq_count;
}
for (size_t i = 0; i < counter; i++)
{
res_global[i + local_offset] = res[i];
}
}
Run Code Online (Sandbox Code Playgroud)
通过这种方法,所有线程在合并时并行工作,并且atomic capture. 请注意,您还可以使用 制作一个简单版本atomic capture,这比关键部分更有效,但仍会很快成为瓶颈:
size_t newq_count_local;
#pragma omp atomic capture
newq_count_local = newq_count++;
newq[newq_count_local] = tgt;
Run Code Online (Sandbox Code Playgroud)
newqcritical您发布的 -version 是错误的,因为index(在外部范围中定义)在线程之间隐式共享。rcvq。否则,您会遇到竞争条件pred[tgt] = src;。pragma omp for循环。另一个答案的想法是正确的。然而,它是 C++,而不是标记为 C。使用std::vector<std::vector<>>. 通常一个向量是用三个指针来实现的,总共24个字节。其中push_back一个指针递增。这意味着,a) 来自多个线程的本地向量的指针驻留在同一高速缓存行上,并且 b) 在每次成功TEST读取push_back和写入其他线程使用的高速缓存行时。该缓存行必须始终在核心之间移动,极大地限制了这种方法的可扩展性。这称为虚假共享。
我根据另一个答案进行了一个小测试,给出了以下性能:
0.99 s- 单线程1.58 s- 同一套接字的两个相邻核心上的两个线程2.13 s- 不同套接字的两个核心上的两个线程0.99 s- 两个线程共享一个核心0.62 s- 两个插槽上有 24 个线程而以上 C 版本的扩展性要好得多:
0.46 s- 单线程(C 与 C++ 没有真正可比性)0.24 s- 两个线程0.04 s- 24 个线程