我从下面用gcc编译的代码中抛出了bad_alloc(尝试4.9.3、5.40和6.2)。 gdb告诉我它发生在unordered_map的initalizer_list的最后一行。如果我注释掉mmx指令_m_maskmovq,则没有错误。同样,如果我注释掉unordered_map的初始化,这也没有错误。仅当调用mmx指令并使用initializer_list初始化unordered_map时,我才得到bad_alloc。如果我默认构造unordered_map并调用map.emplace(1,1),也没有错误。我已经在具有48核(intel xeon)和376 GB RAM的centos7机器上以及在Ubuntu WSL下的Dell笔记本电脑(intel core i7)上运行了该软件,结果相同。这里发生了什么? MMX指令是否在破坏堆? Valgrind似乎没有发现任何有用的东西。

编译器命令和输出:

$g++ -g -std=c++11 main.cpp
$./a.out
   terminate called after throwing an instance of 'std::bad_alloc'
   what():  std::bad_alloc
   Aborted


源代码(main.cpp):

#include <immintrin.h>
#include <unordered_map>

int main()
{
  __m64 a_64 = _mm_set_pi8(0,0,0,0,0,0,0,0);
  __m64 b_64 = _mm_set_pi8(0,0,0,0,0,0,0,0);
  char dest[8] = {0};
  _m_maskmovq(a_64, b_64, dest);

  std::unordered_map<int, int> map{{ 1, 1}};
}


更新:
_mm_empty()解决方法确实解决了此示例。当使用多线程代码(一个线程在执行矢量指令,另一个线程在使用unordered_map)时,这似乎不是可行的解决方案。另一个有趣的问题是,如果我打开-O3的优化功能,bad_alloc就会消失。我们在生产过程中不遗余力,从未遇到过这个错误。

最佳答案

没有堆损坏。发生这种情况是因为std::unordered_map在内部使用long double从初始化程序中的元素数量计算存储桶计数(请参见libstdc ++源代码中的_Prime_rehash_policy::_M_bkt_for_elements)。

从MMX代码切换到FPU代码之前,必须先调用_mm_empty。这与历史性决定有关,即将FPU寄存器重用于MMX寄存器文件(与现代CPU中的寄存器重命名相反)。

如果添加_mm_empty调用,则异常消失:

…
  _m_maskmovq(a_64, b_64, dest);
  _mm_empty();
  std::unordered_map<int, int> map{{ 1, 1}};
…


参见GCC PR 88998,由cpplearner标识。

ongoing work to implement the MMX intrinsics with SSE on x86-64,这将使此问题消失,因为SSE指令不会影响FPU状态,反之亦然。

09-06 23:02