次のコードは、OpenMP 部分の前に CPU アフィニティ マスクを保存し、それを変更して並列領域の期間中すべての CPU を許可してから、以前の CPU アフィニティ マスクを復元する方法の例を示しています。コードは Linux 固有のものであり、 MPI ライブラリによるプロセスの固定を有効にしないと意味がありません。Intel MPI で に設定することで非アクティブ化されます (4.x のデフォルトはプロセスをピン留めすることです)。--bind-to-core
--bind-to-socket
mpiexec
I_MPI_PIN
disable
#define _GNU_SOURCE
#include <sched.h>
...
cpu_set_t *oldmask, *mask;
size_t size;
int nrcpus = 256; // 256 cores should be more than enough
int i;
// Save the old affinity mask
oldmask = CPU_ALLOC(nrcpus);
size = CPU_ALLOC_SIZE(nrcpus);
CPU_ZERO_S(size, oldmask);
if (sched_getaffinity(0, size, oldmask) == -1) { error }
// Temporary allow running on all processors
mask = CPU_ALLOC(nrcpus);
for (i = 0; i < nrcpus; i++)
CPU_SET_S(i, size, mask);
if (sched_setaffinity(0, size, mask) == -1) { error }
#pragma omp parallel
{
}
CPU_FREE(mask);
// Restore the saved affinity mask
if (sched_setaffinity(0, size, oldmask) == -1) { error }
CPU_FREE(oldmask);
...
OpenMP ランタイムの固定引数を微調整することもできます。GCC/libgomp
アフィニティは GOMP_CPU_AFFINITY 環境変数によって制御されますが、Intel コンパイラの場合はKMP_AFFINITYです。OpenMP ランタイムが提供されたアフィニティ マスクとプロセスのアフィニティ マスクを交差する場合でも、上記のコードを使用できます。
完全を期すために、Windows でアフィニティ マスクを保存、設定、および復元します。
#include <windows.h>
...
HANDLE hCurrentProc, hDupCurrentProc;
DWORD_PTR dwpSysAffinityMask, dwpProcAffinityMask;
// Obtain a usable handle of the current process
hCurrentProc = GetCurrentProcess();
DuplicateHandle(hCurrentProc, hCurrentProc, hCurrentProc,
&hDupCurrentProc, 0, FALSE, DUPLICATE_SAME_ACCESS);
// Get the old affinity mask
GetProcessAffinityMask(hDupCurrentProc,
&dwpProcAffinityMask, &dwpSysAffinityMask);
// Temporary allow running on all CPUs in the system affinity mask
SetProcessAffinityMask(hDupCurrentProc, &dwpSysAffinityMask);
#pragma omp parallel
{
}
// Restore the old affinity mask
SetProcessAffinityMask(hDupCurrentProc, &dwpProcAffinityMask);
CloseHandle(hDupCurrentProc);
...
単一のプロセッサ グループ (最大 64 個の論理プロセッサ) で動作する必要があります。