OpenMP: не использовать ядра с гиперпоточностью (половина `num_threads ()` с гиперпоточностью)

Hyper-Threading — это реализация Intel одновременная многопоточность (SMT). Современные процессоры AMD не поддерживают SMT (в семействе микроархитектур Bulldozer есть еще что-то, что AMD называет кластерной многопоточностью, но в микроархитектуре Zen предполагается наличие SMT). OpenMP не имеет встроенной поддержки для обнаружения SMT.

Если вам нужна общая функция для обнаружения Hyper-Threading, вам необходимо поддерживать процессоры разных поколений и убедиться, что процессор является процессором Intel, а не AMD. Для этого лучше всего использовать библиотеку.

Но вы можете создать функцию с использованием OpenMP, которая работает для многих современных процессоров Intel, как я описал Вот.

Следующий код будет подсчитывать количество физических ядер на современных процессорах Intel (он работал на каждом процессоре Intel, на котором я его пробовал). Вы должны связать нити, чтобы заставить это работать. С GCC вы можете использовать
export OMP_PROC_BIND=true в противном случае вы можете связать с кодом (что я и делаю).

Обратите внимание, что я не уверен, что этот метод надежен с VirtualBox. В VirtualBox на 4-ядерном / 8-процессорном процессоре с логическим процессором и Windows в качестве хоста и Linux в качестве догадки устанавливают количество ядер для виртуальной машины на 4, этот код сообщает о 2 ядрах, а / proc / cpuinfo показывает, что два ядра фактически являются логическими процессорами.

#include <stdio.h>

//cpuid function defined in instrset_detect.cpp by Agner Fog (2014 GNU General Public License)
//http://www.agner.org/optimize/vectorclass.zip

// Define interface to cpuid instruction.
// input:  eax = functionnumber, ecx = 0
// output: eax = output[0], ebx = output[1], ecx = output[2], edx = output[3]
static inline void cpuid (int output[4], int functionnumber) {
#if defined (_MSC_VER) || defined (__INTEL_COMPILER)       // Microsoft or Intel compiler, intrin.h included

__cpuidex(output, functionnumber, 0);                  // intrinsic function for CPUID

#elif defined(__GNUC__) || defined(__clang__)              // use inline assembly, Gnu/AT&T syntax

int a, b, c, d;
__asm("cpuid" : "=a"(a),"=b"(b),"=c"(c),"=d"(d) : "a"(functionnumber),"c"(0) : );
output[0] = a;
output[1] = b;
output[2] = c;
output[3] = d;

#else                                                      // unknown platform. try inline assembly with masm/intel syntax

__asm {
mov eax, functionnumber
xor ecx, ecx
cpuid;
mov esi, output
mov [esi],    eax
mov [esi+4],  ebx
mov [esi+8],  ecx
mov [esi+12], edx
}

#endif
}

int getNumCores(void) {
//Assuming an Intel processor with CPUID leaf 11
int cores = 0;
#pragma omp parallel reduction(+:cores)
{
int regs[4];
cpuid(regs,11);
if(!(regs[3]&1)) cores++;
}
return cores;
}

int main(void) {
printf("cores %d\n", getNumCores());
}