- html - 出于某种原因,IE8 对我的 Sass 文件中继承的 html5 CSS 不友好?
- JMeter 在响应断言中使用 span 标签的问题
- html - 在 :hover and :active? 上具有不同效果的 CSS 动画
- html - 相对于居中的 html 内容固定的 CSS 重复背景?
我最近在阅读有关管道优化的文章。我想问一下我是否正确理解了处理器如何处理流水线。
这是简单测试程序的C++代码:
#include <vector>
int main()
{
std::vector<int> vec(10000u);
std::fill(vec.begin(), vec.end(), 0);
for (unsigned i = 0u; i < vec.size(); ++i)
{
vec[i] = 5;
}
return 0;
}
...
00007FF6A4521080 inc edx
{
vec[i] = 5;
00007FF6A4521082 mov dword ptr [rcx+rax*4],5
00007FF6A4521089 mov eax,edx
00007FF6A452108B cmp rax,r9
00007FF6A452108E jb main+80h (07FF6A4521080h)
}
...
cmp rax r9
实际将值分配给eax/rax之前,管道需要等待
mov eax, edx
指令。
最佳答案
TL; DR:
情况1:适合L1D的缓冲区。 vector 构造函数或对std::fill
的调用会将缓冲区完全放在L1D中。在这种情况下,流水线和L1D缓存的每周期1个存储吞吐量是瓶颈。
情况2:适合L2的缓冲区。 vector 构造函数或对std::fill
的调用会将缓冲区完全放置在L2中。但是,L1必须将脏线写回到L2,并且在L1D和L2之间只有一个端口。另外,必须从L2到L1D提取线。 L1D和L2之间的64B/周期带宽应该能够轻松解决这一问题,也许偶尔会有争用(有关更多详细信息,请参见下文)。因此,总体瓶颈与案例1相同。您使用的特定缓冲区大小(大约40KB)不适用于Intel的L1D和最近的AMD处理器,但适合L2。尽管在同时多线程(SMT)的情况下,其他逻辑核心可能会有一些其他争用。
情况3:L2中不适合的缓冲区。这些行需要从L3或内存中获取。 L2 DPL预取器可以跟踪存储并将缓冲区预取到L2中,从而减轻了长等待时间。单个L2端口是L1写回和填充缓冲区的瓶颈。这很严重,特别是当缓冲区不适合L3且互连也可能位于关键路径上时。 1存储吞吐量对于缓存子系统来说太高了。两个最相关的性能计数器是L1D_PEND_MISS.REQUEST_FB_FULL
和和RESOURCE_STALLS.SB
。
首先,请注意vector
本身的构造函数(可能会内联)通过内部调用memset
将元素初始化为零。 memset
基本上与循环执行相同的操作,但已高度优化。换句话说,就大O表示而言,两者的元素数量都是线性的,但是memset
的常数因子较小。此外,std::fill
还内部调用memset
将所有元素设置为零(再次)。 std::fill
也可能会内联(启用适当的优化)。因此,您在那段代码中确实有三个循环。使用std::vector<int> vec(10000u, 5)
初始化 vector 将更加有效。现在让我们进入循环的微体系结构分析。我只会讨论我期望在现代Intel处理器上发生的事情,特别是Haswell和Skylake1。
让我们仔细检查代码:
00007FF6A4521080 inc edx
00007FF6A4521082 mov dword ptr [rcx+rax*4],5
00007FF6A4521089 mov eax,edx
00007FF6A452108B cmp rax,r9
00007FF6A452108E jb main+80h (07FF6A4521080h)
dispatch cycle | allocate cycle
cmp rax,r9 macro-fused | inc edx (iteration J+3)
jb main+80h (07FF6A4521080h) (iteration J) | mov dword ptr [rcx+rax*4],5 (iteration J+3)
mov dword ptr [rcx+rax*4],5 (iteration J+1)| mov eax,edx (iteration J+3)
mov eax,edx (iteration J+1)| cmp rax,r9 macro-fused
inc edx (iteration J+2)| jb main+80h (07FF6A4521080h) (iteration J+3)
---------------------------------------------------------|---------------------------------------------------------
cmp rax,r9 macro-fused | inc edx (iteration J+4)
jb main+80h (07FF6A4521080h) (iteration J+1)| mov dword ptr [rcx+rax*4],5 (iteration J+4)
mov dword ptr [rcx+rax*4],5 (iteration J+2)| mov eax,edx (iteration J+4)
mov eax,edx (iteration J+2)| cmp rax,r9 macro-fused
inc edx (iteration J+3)| jb main+80h (07FF6A4521080h) (iteration J+4)
cmp
和
jb
指令将被宏融合到单个uop中。因此,在融合域中,微指令的总数为4,在非融合域中为5。他们之间只有一跳。因此,每个循环可以发出一个单循环迭代。
inc
和
mov
-store之间的依赖性,因此无法在同一周期内分派(dispatch)这两条指令。但是,可以使用来自先前迭代的uops调度来自先前迭代的
inc
。
inc
和
mov
分配到四个端口(p0,p1,p5,p6)。预测采用的
cmp/jb
恰好有一个端口p6。
mov dword ptr [rcx+rax*4],5
的STA uop有三个端口(p2,p3,p7),而STD uop有一个端口p4。 (尽管p7无法处理指定的寻址模式。)由于每个端口只有一个端口,因此可以实现的最大执行吞吐量是每个周期1次迭代。
L1D_PEND_MISS.REQUEST_FB_FULL
和和
RESOURCE_STALLS.SB
。
memset
的两次调用。
mov dword ptr [rcx+rax*4],5
will get unlaminiated,在融合域中每次迭代产生5 oups。因此,前端可能位于关键路径上。
关于c++ - 寄存器流水线计算,我们在Stack Overflow上找到一个类似的问题: https://stackoverflow.com/questions/52280958/
我无法理解如何使用一些旧的 VGA 代码在这个示例中设置序列 Controller 寄存器: mov dx,SC_INDEX mov ax,0604h out dx,ax
我希望对 zmm 0-31 寄存器集的四字元素执行整数算术运算并保留这些运算产生的进位位。看来这只有在通用寄存器集中处理数据时才有可能。 因此,我想将信息从 zmm 0-31 寄存器之一复制到通用寄存
ARM 64中包含多种寄存器,下面介绍一些常见的寄存器。 1 通用寄存器 ARM 64包含31个64bit寄存器,记为X0~X30。 每一个通用寄存器,它的低32bit都可以被访问,记为W0~W
1.寄存器 组合逻辑存在一个最大的缺点就是存在竞争与冒险,系统会产生不定态;使用时序逻辑电路就会极大的改善这种情况 寄存器具有存储功能,一般是由D触发器构成,由时钟脉冲控制,每个D触发器能够
使用 $gp 是否存在危险?注册以存储值?我想我的问题是 $gp 的真正功能是什么?它是否以某种方式在幕后调用,以便如果我使用它,事情可能会变得非常非常错误? 最佳答案 那么,$gp register
我遇到了这段代码的问题,我无法弄清楚问题出在哪里。所以当我运行这段代码时:if $row["count"] > 0 else块运行和 $_SESSION["error"]设置。 当$row["coun
所以我正在做二进制炸弹的变体。这就是阶段 0x0000000000401205 : sub $0x8,%rsp 0x0000000000401209 : cmp $0x3,
我在一个名为 (EmployeeDetailKey - varchar(10)) 的字段中获得了一个值,其中包含顺序值,例如 00001, 00002, 00003.... 它位于 Employeed
我有一个要求,应该为每个调用的线程分配一个计数器变量。但我没有得到预期的结果,实际上计数器在线程中重复。我创建了一个虚拟表和一个过程来将计数器值插入到表中。无论如何,是否可以更改代码以便线程获得递增的
预期输出:需要打印第4季度的wage_amt +--------------+--------------+--------------+--------------+ | wages_amt_q1
如何匹配模式 abc_[someArbitaryStringHere]_xyz? 为了澄清,我希望正则表达式能够匹配以下性质的字符串: abc_xyz、abc_asdfsdf_xyz、abc_32rw
从下拉列表(自定义)中选择一个值而不是常规下拉列表,它有很多下拉值 我可以用代码选择第一个值 find('.selected', :text=>arg1,exact: false).click 但无法
这个问题不太可能帮助任何 future 的访问者;它只与一个小的地理区域、一个特定的时间点或一个非常狭窄的情况有关,这些情况并不普遍适用于互联网的全局受众。为了帮助使这个问题更广泛地适用,visit
我有 .csv 文件中的数据,它包含 2 列 x 轴和 y 轴。从 .csv 文件读取轴,然后使用拉伸(stretch)指数函数拟合数据,但显示错误。 这里我给出示例数据以方便理解。 我的函数是f(x
我正在尝试使用以下汇编代码将磁盘扇区加载到内存中,但正如我在终端中使用一些 int 0x10 时发现的那样,它不起作用的原因是它陷入了无限循环。我以为循环会自动为我递减 cx 寄存器。下面是代码,其中
我正在尝试编写一个脚本,该脚本将在 vim 中打开一个文件并将其中的特定行复制到 vim 的寄存器之一中。当脚本再次运行时,它会决定再次打开文件,然后将 vim 寄存器中的值粘贴回。实际上,脚本应该在
我目前正在尝试弄清楚如何将指针寄存器 SI 指向的内存中的第一个字节添加到 AX 寄存器的当前内容中。 因此,如果 SI 包含某个地址,并且该地址在内存中的值是:00 和 01,我希望将 00 添加到
我试图将两个 16 位数字与以下 NASM 代码相乘: mov ax, [input1] mov bx, [input2] mul bx 前面代码的结果存储在 DX:AX 我试图使用来自单独库“pri
我正在尝试修改 rip 寄存器(只是为了好玩)。 buffer 应该是内存地址,所以不知道为什么会得到Error: operand type mismatch for 'movq' #include
我可以告诉gcc-style inline assembly把我的__m512i变量到特定 zmm注册,如 zmm31 ? 最佳答案 就像在根本没有特定寄存器约束的目标(如 ARM)上一样,使用 lo
我是一名优秀的程序员,十分优秀!