- html - 出于某种原因,IE8 对我的 Sass 文件中继承的 html5 CSS 不友好?
- JMeter 在响应断言中使用 span 标签的问题
- html - 在 :hover and :active? 上具有不同效果的 CSS 动画
- html - 相对于居中的 html 内容固定的 CSS 重复背景?
幸运的是,PTEST
不会影响进位标志,而只会设置(相当尴尬的)ZF。还会影响 CF 和 ZF。
我提出了以下序列来测试大量值,但我对糟糕的运行时间感到不满意。
Latency / rThoughput
setup:
xor eax,eax ; na
vpxor xmm0,xmm0 ; na ;mask to use for the nand operation of ptest
work:
vptest xmm4,xmm0 ; 3 1 ;is xmm4 alive?
adc eax,eax ; 1 1 ;move first bit into eax
vptest xmm5,xmm0 ; 3 1 ;is N alive?
adc eax,eax ; 1 1 ;move consecutive bits into eax
我想要在eax
中拥有所有非零寄存器的位图(显然我可以在多个寄存器中组合多个位图)。
因此每个测试都有 3+1 = 4 个周期的延迟。
其中一些可以通过在 eax
、ecx
等之间交替来并行运行。
但还是很慢。
有没有更快的方法来做到这一点?
我需要连续测试 8 个 xmm/ymm 寄存器。一字节位图中每个寄存器 1 位。
最佳答案
实际上,您现有的方法并不是“相当慢”,而是合理的。
当然,每个单独的测试都有 4 个周期的延迟1,但如果您希望将结果保存在通用寄存器中,您通常需要支付 3 个周期的费用无论如何,该移动的延迟(例如,movmskb
的延迟也为 3)。无论如何,您想要测试 8 个寄存器,并且不能简单地添加延迟,因为每个寄存器基本上都是独立的,因此 uop 计数和端口使用最终可能比测试单个寄存器的延迟更重要。的延迟将与其他工作重叠。
在英特尔硬件上可能更快一点的方法是使用连续的 PCMPEQ
指令来测试多个向量,然后将结果折叠在一起(例如,如果您使用 PCMPEQQ,您实际上可以得到4 个四字结果,需要将它们折叠成 1)。您可以在 PCMPEQ
之前或之后折叠,但这有助于更多地了解您希望如何/在何处获得更好的结果。这是 8 个寄存器的未经测试的草图,xmm1-8
中的 xmm0
假定为零,xmm14
是 pblendvb
掩码选择最后一条指令中使用的替代字节。
# test the 2 qwords in each vector against zero
vpcmpeqq xmm11, xmm1, xmm0
vpcmpeqq xmm12, xmm3, xmm0
vpcmpeqq xmm13, xmm5, xmm0
vpcmpeqq xmm14, xmm7, xmm0
# blend the results down into xmm10 word origin
vpblendw xmm10, xmm11, xmm12, 0xAA # 3131 3131
vpblendw xmm13, xmm13, xmm14, 0xAA # 7575 7575
vpblendw xmm10, xmm10, xmm13, 0xCC # 7531 7531
# test the 2 qwords in each vector against zero
vpcmpeqq xmm11, xmm2, xmm0
vpcmpeqq xmm12, xmm4, xmm0
vpcmpeqq xmm13, xmm6, xmm0
vpcmpeqq xmm14, xmm8, xmm0
# blend the results down into xmm11 word origin
vpblendw xmm11, xmm11, xmm12, 0xAA # 4242 4242
vpblendw xmm13, xmm13, xmm14, 0xAA # 8686 8686
vpblendw xmm11, xmm11, xmm13, 0xCC # 8642 8642
# blend xmm10 and xmm11 together int xmm100, byte-wise
# origin bytes
# xmm10 77553311 77553311
# xmm11 88664422 88664422
# res 87654321 87654321
vpblendvb xmm10, xmm10, xmm11, xmm15
# move the mask bits into eax
vpmovmskb eax, xmm10
and al, ah
直觉是,您将每个 xmm
中的每个 QWORD
与零进行测试,为 8 个寄存器提供 16 个结果,然后将结果混合到 中xmm10
按顺序每个字节得到一个结果(所有高 QWORD 结果在所有低 QWORD 结果之前)。然后,您使用 movmskb
将这些 16 字节掩码作为 16 位移动到 eax
中,最后将每个寄存器的高和低 QWORD
位结合起来 eax
。
在我看来,8 个寄存器总共有 16 个微指令,所以每个寄存器大约有 2 个微指令。总延迟是合理的,因为它主要是“减少”类型的并行树。一个限制因素是 6 个 vpblendw
操作,它们都只发送到现代 Intel 上的端口 5。最好用 VPBLENDD
替换其中的 4 个,这是一个适用于 p015
中任何一个的“祝福”混合物。这应该很简单。
所有操作都简单快速。最后的和al, ah
是部分寄存器写入,但是如果你在eax
之后mov
它也许没有惩罚。如果这是一个问题,您也可以通过几种不同的方式来完成最后一行...
这种方法也可以自然地扩展到 ymm
寄存器,但最后的 eax
折叠略有不同。
编辑
稍快的结局使用打包移位来避免两条昂贵的指令:
;combine bytes of xmm10 and xmm11 together into xmm10, byte wise
; xmm10 77553311 77553311
; xmm11 88664422 88664422 before shift
; xmm10 07050301 07050301
; xmm11 80604020 80604020 after shift
;result 87654321 87654321 combined
vpsrlw xmm10,xmm10,8
vpsllw xmm11,xmm11,8
vpor xmm10,xmm10,xmm11
;combine the low and high dqword to make sure both are zero.
vpsrldq xmm12,xmm10,64
vpand xmm10,xmm12
vpmovmskb eax,xmm10
这通过避免 2 个周期 vpblendvb
和 or al,ah
的部分写入惩罚节省了 2 个周期,它还修复了对慢速 vpmovmskb 的依赖
如果不需要立即使用该指令的结果。
1实际上,PTEST
似乎仅在 Skylake 上有 3 个周期的延迟,在此之前似乎是 2 个周期。我也不确定您为 rcl eax, 1
列出的 1 个周期延迟:根据 Agner 的说法,在现代英特尔上,它似乎是 3 uops 和 2 个周期延迟/recip 吞吐量。
关于assembly - 测试 xmm/ymm 寄存器是否为零的更快方法?,我们在Stack Overflow上找到一个类似的问题: https://stackoverflow.com/questions/42317528/
我无法理解如何使用一些旧的 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
我是一名优秀的程序员,十分优秀!