- iOS/Objective-C 元类和类别
- objective-c - -1001 错误,当 NSURLSession 通过 httpproxy 和/etc/hosts
- java - 使用网络类获取 url 地址
- ios - 推送通知中不播放声音
我正在 haswell 中试验 tsx 扩展,通过调整现有的中型(1000 行)代码库以使用 GCC 事务内存扩展(在 native 中间接使用 haswell tsx)而不是粗粒度锁。我正在使用 GCC 的 transactional_memory 扩展,而不是直接编写我自己的 _xbegin/_xend。我正在使用 ITM_DEFAULT_METHOD=htm
我在让它足够快地工作时遇到了问题,因为由于神秘的原因,我的硬件事务中止率很高。如下所示,这些中止不是由于冲突,也不是由于容量限制。
下面是我用来量化故障率和根本原因的 perf 命令:
perf stat \
-e cpu/event=0x54,umask=0x2,name=tx_mem_abort_capacity_write/ \
-e cpu/event=0x54,umask=0x1,name=tx_mem_abort_conflict/ \
-e cpu/event=0x5d,umask=0x1,name=tx_exec_misc1/ \
-e cpu/event=0x5d,umask=0x2,name=tx_exec_misc2/ \
-e cpu/event=0x5d,umask=0x4,name=tx_exec_misc3/ \
-e cpu/event=0x5d,umask=0x8,name=tx_exec_misc4/ \
-e cpu/event=0x5d,umask=0x10,name=tx_exec_misc5/ \
-e cpu/event=0xc9,umask=0x1,name=rtm_retired_start/ \
-e cpu/event=0xc9,umask=0x2,name=rtm_retired_commit/ \
-e cpu/event=0xc9,umask=0x4,name=rtm_retired_aborted/pp \
-e cpu/event=0xc9,umask=0x8,name=rtm_retired_aborted_misc1/ \
-e cpu/event=0xc9,umask=0x10,name=rtm_retired_aborted_misc2/ \
-e cpu/event=0xc9,umask=0x20,name=rtm_retired_aborted_misc3/ \
-e cpu/event=0xc9,umask=0x40,name=rtm_retired_aborted_misc4/ \
-e cpu/event=0xc9,umask=0x80,name=rtm_retired_aborted_misc5/ \
./myprogram -th 1 -reps 3000000
因此,该程序运行了一些包含交易的代码 3000 万次。每个请求涉及一个事务 gcc __transaction_atomic
block 。此运行中只有一个线程。
这个特殊的 perf
命令捕获了 Intel software developers manual vol 3 中描述的大部分相关 tsx 性能事件。 .
perf stat
的输出如下:
0 tx_mem_abort_capacity_write [26.66%]
0 tx_mem_abort_conflict [26.65%]
29,937,894 tx_exec_misc1 [26.71%]
0 tx_exec_misc2 [26.74%]
0 tx_exec_misc3 [26.80%]
0 tx_exec_misc4 [26.92%]
0 tx_exec_misc5 [26.83%]
29,906,632 rtm_retired_start [26.79%]
0 rtm_retired_commit [26.70%]
29,985,423 rtm_retired_aborted [26.66%]
0 rtm_retired_aborted_misc1 [26.75%]
0 rtm_retired_aborted_misc2 [26.73%]
29,927,923 rtm_retired_aborted_misc3 [26.71%]
0 rtm_retired_aborted_misc4 [26.69%]
176 rtm_retired_aborted_misc5 [26.67%]
10.583607595 seconds time elapsed
从输出中可以看出:
rtm_retired_start
计数为 3000 万(匹配程序的输入)rtm_retired_abort
计数大致相同(根本没有提交)abort_conflict
和abort_capacity
计数为 0,所以这些不是原因。另外,回想一下,它只有一个线程在运行,冲突应该很少见。tx_exec_misc1
和 rtm_retired_aborted_misc3
的高值,它们在描述上有些相似。Intel 手册(第 3 卷)定义了 rtm_retired_aborted_misc3
计数器:
code: C9H 20H
mnemonic: RTM_RETIRED.ABORTED_MISC3
description: Number of times an RTM execution aborted due to HLE unfriendly instructions.
tx_exec_misc1
的定义有一些相似的话:
code: 5DH 01H
mnemonic: TX_EXEC.MISC1
description: Counts the number of times a class of instructions that may cause a transactional abort was executed. Since this is the count of execution, it may not always cause a transactional abort.
我使用对 rtm_retired_aborted
的高精度 (PEBS) 支持使用 perf record/perf report 检查了中止的装配位置。该位置有一条从寄存器到寄存器的 mov
指令。附近没有看到奇怪的指令名称。
更新:
这是我从那时起尝试过的两件事:
1) 我们在这里看到的 tx_exec_misc1 和 rtm_retired_aborted_misc3 签名可以通过例如以下形式的虚拟 block 获得
for (int i = 0; i < 10000000; i++){
__transaction_atomic{
_xabort(1);
}
}
或其中一种形式
for (int i = 0; i < 10000000; i++){
__transaction_atomic{
printf("hello");
fflush(stdout);
}
}
在这两种情况下,性能计数器看起来都与我看到的相似。然而,在这两种情况下,-e cpu/tx-abort/
的 perf report
都指向直观正确的装配线:一个 xabort
指令第一个示例和第二个示例的 syscall
。在真实的代码库中,perf 报告指向函数开始时的堆栈推送:
: 00000000004167e0 <myns::myfun()>:
100.00 : 4167e0: push %rbp
0.00 : 4167e1: mov %rsp,%rbp
0.00 : 4167e4: push %r15
我也在intel软件开发模拟器下运行了同样的命令。事实证明,在那种情况下问题就消失了:就应用程序而言,我没有中止。
最佳答案
虽然这种情况已经有一段时间了,但我在搜索时发现了这个悬而未决的问题,所以这是答案:这是 Haswell 和早期 Broadwell 芯片中的硬件错误。
Intel 指定的特定硬件错误是 HSW136 ,并且无法使用微码更新修复。事实上,我认为正是在第 4 步中,该功能不再被 cpuid
指令报告为可用,即使芯片上存在(故障)芯片来实现它也是如此。
关于c++ - 使用 haswell tsx 的神秘 rtm 中止,我们在Stack Overflow上找到一个类似的问题: https://stackoverflow.com/questions/30069492/
我在 Haswell CPU(Intel Core i7-4790)上安装了 perf。但“性能列表”不包括“stalled-cycles-frontend”或“stalled-cycles-back
关闭。这个问题不满足Stack Overflow guidelines .它目前不接受答案。 想改善这个问题吗?更新问题,使其成为 on-topic对于堆栈溢出。 7年前关闭。 Improve thi
我正在使用 Intel Haswell CPU 的 FMA 指令来优化一些计算。 但是,我发现即使我将 MXCSR 寄存器设置为 DNZ 和 FTZ 模式,这些指令也会生成异常。 我如何强制这些 FM
哪些编译器(截至 2014 年 5 月)能够生成使用事务内存功能(受限事务内存,而不仅仅是锁省略)的代码? 最佳答案 GCC,截至 version 4.8支持英特尔 RTM: Support for
我正在尝试使用自上而下的微架构分析方法 (TMAM) 来分析 Intel Haswell CPU (Intel® Core™ i7-4900MQ) 上的执行情况,如 Intel® 64 and IA-
在准备一些演示文稿时,我突然想到,我不知道 Haswell 内核一次可以执行的整数运算数量的理论限制是多少。 我曾经天真地假设“Intel 内核具有 HT,但这可能会并行化不同类型的工作,因此内核可能
要知道,haswell是英特尔作为Ivy Bridge微架构的“第四代核心”继承者而开发的一种处理器微架构的代号。 1英特尔正式发布了基于这种微架构的CPU... More 但是,我想知道如何通过在
这个循环在 Intel Conroe/Merom 上每 3 个周期运行一次迭代,如预期的那样在 imul 吞吐量上出现瓶颈。但是在 Haswell/Skylake 上,它每 11 个周期运行一次迭代,
我正在查看AVX programming reference 。 new Haswell instructions包括一些期待已久的“聚集”负载。但是,我无法弄清楚索引数据项的对齐限制是什么。引用文献
我编写了一些在 Haswell i7 处理器上运行的 AVX2 代码。相同的代码库也用于非 Haswell 处理器,其中相同的代码应替换为它们的 SSE 等效项。我想知道编译器是否有办法忽略非 Has
在英特尔内部函数指南中,vmulpd和vfmadd213pd延迟为 5,vaddpd延迟为 3。 我编写了一些测试代码,但所有结果都慢了 1 个周期。 这是我的测试代码: .CODE test_lat
在英特尔内部函数指南中,vmulpd和vfmadd213pd延迟为 5,vaddpd延迟为 3。 我编写了一些测试代码,但所有结果都慢了 1 个周期。 这是我的测试代码: .CODE test_lat
我目前正在使用 Intel Haswell RTM(事务内存的硬件支持)开发应用程序。据我所知here和 here ,建议的过程是使用某种回退锁,以防事务中止。 推荐流程如下: someTypeOfL
关闭。这个问题需要debugging details .它目前不接受答案。 编辑问题以包含 desired behavior, a specific problem or error, and th
我正在 haswell 中试验 tsx 扩展,通过调整现有的中型(1000 行)代码库以使用 GCC 事务内存扩展(在 native 中间接使用 haswell tsx)而不是粗粒度锁。我正在使用 G
我有以下代码(正常、SSE 和 AVX): int testSSE(const aligned_vector & ghs, const aligned_vector & lhs) { int
GCC 支持 __builtin_clz(int x) 内置函数,它计算参数中前导零(连续的最高有效零)的数量。 除其他外0,这对于有效实现 lg(unsigned int x) 非常有用函数,取 x
我正在使用 AVX 一次计算八个点积。在我当前的代码中,我做了这样的事情(在展开之前): Ivy 桥/沙桥 __m256 areg0 = _mm256_set1_ps(a[m]); for(int i
我对使用 Sandy-Bridge 和 Haswell 可以完成每个内核每个周期的触发器感到困惑。 根据我对 SSE 的理解,SSE 的每个内核每个周期应该是 4 个触发器,AVX/AVX2 的每个内
我编写了很多 punpckl、pextrd 和 pinsrd 的代码,它们旋转 8x8 字节矩阵,作为使用循环平铺旋转 B/W 图像的更大例程的一部分。 我使用 IACA 对其进行了分析,以查看是否值
我是一名优秀的程序员,十分优秀!