- html - 出于某种原因,IE8 对我的 Sass 文件中继承的 html5 CSS 不友好?
- JMeter 在响应断言中使用 span 标签的问题
- html - 在 :hover and :active? 上具有不同效果的 CSS 动画
- html - 相对于居中的 html 内容固定的 CSS 重复背景?
我想知道在任何 SIMD 指令系列中是否可以执行以下操作。
我有一个具有 63 个有效位(从不为负)的 qword 输入。从 LSB 开始的每个连续的 7 位都被混洗对齐到一个字节,左填充为 1(除了最重要的非零字节)。为了说明,为了清楚起见,我将使用字母。
结果只有有效字节,因此大小为 0 - 9,它被转换为字节数组。
In: 0|kjihgfe|dcbaZYX|WVUTSRQ|PONMLKJ|IHGFEDC|BAzyxwv|utsrqpo|nmlkjih|gfedcba
Out: 0kjihgfe|1dcbaZYX|1WVUTSRQ|1PONMLKJ|1IHGFEDC|1BAzyxwv|1utsrqpo|1nmlkjih|1gfedcba
大小 = 9
In: 00|nmlkjih|gfedcba
Out: |0nmlkjih|1gfedcba
大小 = 2
我知道填充是分开的。洗牌对齐是我的问题。这可能吗?
编辑 2
这是我更新的代码。在单线程 Core 2 Duo 2 GHz,64 位上获得持续 46 M/秒的随机长度输入。
private static int DecodeIS8(long j, ref byte[] result)
{
if (j <= 0)
{
return 0;
}
int size;
// neater code: gives something to break out of
while (true)
{
result[0] = (byte)((j & 0x7F) | 0x80);
size = 0;
j >>= 7;
if (j == 0) break;
result[1] = (byte)((j & 0x7F) | 0x80);
size++;
j >>= 7;
if (j == 0) break;
result[2] = (byte)((j & 0x7F) | 0x80);
size++;
j >>= 7;
if (j == 0) break;
result[3] = (byte)((j & 0x7F) | 0x80);
size++;
j >>= 7;
if (j == 0) break;
result[4] = (byte)((j & 0x7F) | 0x80);
size++;
j >>= 7;
if (j == 0) break;
result[5] = (byte)((j & 0x7F) | 0x80);
size++;
j >>= 7;
if (j == 0) break;
result[6] = (byte)((j & 0x7F) | 0x80);
size++;
j >>= 7;
if (j == 0) break;
result[7] = (byte)((j & 0x7F) | 0x80);
size++;
j >>= 7;
if (j == 0) break;
result[8] = (byte)j;
return 9;
}
result[size] ^= 0x80;
return size + 1;
}
最佳答案
是的,可以使用 MMX/SSE 的 pmullw
指令(内部函数:_mm_mullo_pi16
)进行逐元素移位。
基本思想是使用 AND 指令提取交替的 7 位元素,并执行 pmullw
将元素移位到位。这将完成一半元素的任务,因此需要通过几个额外的类次重复该过程。
#include <stdio.h>
#include <stdint.h>
#include <mmintrin.h>
__m64 f(__m64 input) {
static const __m64 mask = (__m64) 0xfe03f80fe03f80UL;
static const __m64 multiplier = (__m64) 0x0080002000080002UL;
__m64 t0 = _mm_and_si64 (input, mask);
__m64 t1 = _mm_and_si64 (_mm_srli_si64 (input, 7), mask);
t0 = _mm_mullo_pi16 (t0, multiplier);
t1 = _mm_mullo_pi16 (t1, multiplier);
__m64 res = _mm_or_si64 (t0, _mm_slli_si64 (t1, 8));
/* set most significant bits, except for in most significant byte */
return _mm_or_si64 (res, (__m64) 0x0080808080808080UL);
}
int main(int argc, char *argv[])
{
int i;
typedef union {
__m64 m64;
unsigned char _8x8[8];
} type_t;
/* 0x7f7e7c7870608080 = {127, 63, 31, 15, 7, 3, 2, 1, 0} */
type_t res0 = { .m64 = f((__m64) 0x7f7e7c7870608080UL) };
for (i = 0; i < 8; i++) {
printf("%3u ", res0._8x8[i]);
}
puts("");
return 0;
}
掩码
提取交替的 7 位元素。 multiplier
是一个常量,它允许我们指定每个元素的移位。它源自查看屏蔽输入:
00000000|dcbaZYX0|000000PO|NMLKJ000|0000BAzy|xwv00000|00nmlkji|h0000000
并意识到这一点
00000000|dcbaZYX0 needs to be shifted by 7 (or multiplied by 2^7, 128, 0x0080)
000000PO|NMLKJ000 needs to be shifted by 5 (or multiplied by 2^5, 32, 0x0020)
0000BAzy|xwv00000 needs to be shifted by 3 (or multiplied by 2^3, 8, 0x0008)
00nmlkji|h0000000 needs to be shifted by 1 (or multiplied by 2^1, 2, 0x0002)
此函数一次写入 8 个字节(而不是 9 个 7 位元素将解压缩到的 9 个字节),因此每次迭代后您只需将源指针前进 7 个字节。因此,转换为 SSE2 有点复杂。
我不认为可以为 t1
使用不同的掩码和乘数来避免移位,因为 t1
的元素将跨越 16 位边界,这将阻止 pmullw
工作。但是,仍然有可能以某种方式进行优化。
我没有对此进行基准测试,但我怀疑它比您的标量版本快得多。如果您对其进行基准测试,请发布结果。我很想看看他们。
总而言之,该算法是 2 次移位、2 次 OR、2 次与和两次乘法(以及一些移动)以生成 8 字节。
关于x86 - QWORD 将连续的 7 位洗牌到字节对齐与 SIMD SSE...AVX,我们在Stack Overflow上找到一个类似的问题: https://stackoverflow.com/questions/10850054/
关闭。这个问题不符合Stack Overflow guidelines .它目前不接受答案。 想改进这个问题?将问题更新为 on-topic对于堆栈溢出。 7年前关闭。 Improve this qu
我有一个代码库,我可以在我的 mac 上编译和运行,但不能在我的远程 linux 机器上编译和运行,我不确定为什么。 编译时出现错误 fatal error: simd/simd.h: No such
我需要了解如何编写一些可并行化问题的 C++ 跨平台实现,以便在可用的情况下利用 SIMD(SSE、SPU 等)。以及我希望能够在运行时在 SIMD 和非 SIMD 之间切换。 您建议我如何解决这个问
我正在使用 AVX 内在 _mm256_extract_epi32() . 不过,我不完全确定我是否正确使用它,因为 gcc 不喜欢我的代码,而 clang 编译它并运行它没有问题。 我根据整数变量的
当我可以使用 SSE3 或 AVX 时,SSE2 或 MMX 等较旧的 SSE 版本是否可用 - 还是我还需要单独检查它们? 最佳答案 一般来说,这些都是附加的,但请记住,多年来英特尔和 AMD 对这
在 godbolt.org 使用 gcc 7.2 我可以看到以下内容 code在汇编程序中翻译得非常好。我看到 1 次加载、1 次添加和 1 次存储。 #include __attribute__(
假设我们有一个函数将两个数组相乘,每个数组有 1000000 个 double 值。在 C/C++ 中,该函数如下所示: void mul_c(double* a, double* b) {
我有一个 A = a1 a2 a3 a4 b1 b2 b3 b4 c1 c2 c3 c4 d1 d2 d3 d4 我有两排, float32x2_t a = a1 a2 flo
我正在考虑编写一个 SIMD vector 数学库,因此作为一个快速基准,我编写了一个程序,该程序执行 1 亿(4 个 float ) vector 元素乘法并将它们加到累积总数中。对于我的经典非 S
我正在开发带有英特尔编译器 OpenMP 4.0 的英特尔 E5(6 核、12 线程) 为什么这段代码 SIMD 编译比并行 SIMD 编译更快? for (int suppv = 0; suppv
OpenMP 4.0 引入了 SIMD 结构以利用 CPU 的 SIMD 指令。根据规范http://www.openmp.org/mp-documents/OpenMP4.0.0.pdf ,有两种结
英特尔编译器允许我们通过以下方式对循环进行矢量化 #pragma simd for ( ... ) 但是,您也可以选择使用 OpenMP 4 的指令执行此操作: #pragma omp simd fo
关注我的 x86 question ,我想知道如何在 Arm-v8 上有效地矢量化以下代码: static inline uint64_t Compress8x7bit(uint64_t x) {
Intel 提供了几个 SIMD 命令,它们似乎都对 128 位数据执行按位异或: _mm_xor_pd(__m128d, __m128d) _mm_xor_ps(__m128, __m128) _m
可以使用“位打包”技术压缩无符号整数:在一个无符号整数 block 中,只存储有效位,当一个 block 中的所有整数都“小”时,会导致数据压缩。该方法称为 FOR (引用框架)。 有SIMD lib
SSE 寄存器是否在逻辑处理器(超线程)之间共享或复制? 对于 SSE 繁重的程序,我能否期望从并行化中获得与普通程序相同的加速(英特尔声称具有超线程的处理器为 30%)? 最佳答案 从英特尔的文档中
我正在编写一个使用 SSE 指令来乘法和相加整数值的程序。我用浮点数做了同样的程序,但我的整数版本缺少一个指令。 使用浮点数,在完成所有操作后,我将 de 值返回到常规浮点数数组,执行以下操作: _m
我正在开发基于Intel指令集(AVX,FMA等)的高性能算法。当数据按顺序存储时,我的算法(内核)运行良好。但是,现在我面临一个大问题,但没有找到解决方法或解决方案: see 2D Matrix i
大家好 :) 我正在尝试了解有关浮点、SIMD/数学内在函数和 gcc 的快速数学标志的一些概念。更具体地说,我在 x86 cpu 上使用 MinGW 和 gcc v4.5.0。 我已经搜索了一段时间
根据https://sourceware.org/glibc/wiki/libmvec GCC 具有数学函数的向量实现。它们可以被编译器用于优化,可以在这个例子中看到:https://godbolt.
我是一名优秀的程序员,十分优秀!