草庐IT

c++ - 使用英特尔 AVX 通过掩码改组

coder 2023-11-17 原文

我是 AVX 编程的新手。我有一个需要洗牌的寄存器。我想将几个字节从 256 位寄存器 R1 混洗到空寄存器 R2。我想定义一个掩码，它告诉混洗操作应该将旧寄存器(R1)中的哪个字节复制到新寄存器的哪个位置。

掩码应如下所示(R1 中的 Src:Byte Pos，R2 中的 Target:Byte Pos):

{(0,0),(1,1),(1,4),(2,5),...}

这意味着几个字节被复制了两次。

我不是 100% 确定我应该为此使用哪个函数。我尝试了这两个 AVX 功能，第二个只使用了 2 个 channel 。
__m256 _mm256_permute_ps (__m256 a, int imm8)
__m256 _mm256_shuffle_ps (__m256 a, __m256 b, const int imm8)

我对 imm8 中的 Shuffle Mask 以及如何设计它以使其按上述方式工作感到非常困惑。

我看过这个 slides (第 26 页)描述了 _MM_SHUFFLE，但我找不到解决我的问题的方法。

有没有关于如何设计这样一个面具的教程？或者两种方法的示例函数以深入理解它们？

提前感谢您的提示

最佳答案

TL:DR:您可能需要多次洗牌来处理车道交叉，或者如果您的模式完全如此，您可以使用 _mm256_cvtepu16_epi32 ( vpmovzxwd ) 然后是 _mm256_blend_epi16 .

对于 x86 shuffle(我认为像大多数 SIMD 指令集一样)，目标位置是隐式的。 shuffle-control 常量只有目标顺序中的源索引，是否是 imm8它被编译+组装成一个 asm 指令，或者它是否是一个在每个元素中都有一个索引的 vector 。

每个目标位置恰好读取一个源位置，但可以多次读取同一个源位置。每个目标元素从 shuffle 源获取一个值。

见 Convert _mm_shuffle_epi32 to C expression for the permutation?对于 dst = _mm_shuffle_epi32(src, _MM_SHUFFLE(d,c,b,a)) 的普通 C 版本，显示如何使用控制字节。

(对于 pshufb/_mm_shuffle_epi8 ，具有高位的元素将该目标位置设置为零而不是读取任何源元素，但其他 x86 shuffle 会忽略 shuffle 控制 vector 中的所有高位。)

如果没有 AVX512 合并掩码，就没有混合到目的地的洗牌。有一些双源洗牌，如 _mm256_shuffle_ps ( vshufps ) 可以将来自两个源的元素混洗在一起以生成单个结果 vector 。 如果您想保留一些未写入的目标元素，您可能必须先洗牌，然后再混合 ，例如与 _mm256_blendv_epi8 ，或者如果您可以使用 16 位粒度的混合，则可以使用更有效的立即混合 _mm256_blend_epi16 ，甚至更好 _mm256_blend_epi32 (AVX2 vpblendd 在 Intel CPU 上与 _mm256_and_si256 一样便宜，如果您确实需要混合，如果它可以完成工作，则是最佳选择；请参阅 http://agner.org/optimize/ )

对于您的问题(Cannonlake 中没有 AVX512VBMI vpermb)，您不能将单个字节从 __m256i 的低 16 个“ channel ”混洗到高 16 个“ channel ”中具有单个操作的 vector 。

AVX shuffle 不像完整的 256 位 SIMD，它们更像是两个 128 位并行操作。唯一的异常(exception)是一些具有 32 位或更大粒度的 AVX2 车道交叉洗牌，例如 vpermd ( _mm256_permutevar8x32_epi32 )。还有pmovzx的AVX2版本/pmovsx ，例如pmovzxbq确实将 XMM 寄存器的低 4 字节零扩展到 YMM 寄存器的 4 个 qword，而不是 YMM 寄存器每一半的低 2 字节。这使得它对内存源操作数更有用。

但无论如何，pshufb的AVX2版本( _mm256_shuffle_epi8 ) 在 256 位 vector 的两个 channel 中执行两个单独的 16x16 字节混洗。

你可能会想要这样的东西 :

// Intrinsics have different types for integer, float and double vectors
// the asm uses the same registers either way
__m256i  shuffle_and_blend(__m256i dst, __m256i src)
{
    // setr takes element in low to high order, like a C array init
    // unlike the standard Intel notation where high element is first
    const __m256i  shuffle_control = _mm256_setr_epi8(
          0,      1,  -1, -1,   1,      2, ...);
    // {(0,0),  (1,1), (zero)  (1,4), (2,5),...}  in your src,dst notation
    // Use -1 or 0x80 or anything with the high bit set
    //  for positions you want to leave unmodified in dst
   // blendv uses the high bit as a blend control, so the same vector can do double duty

    // maybe need some lane-crossing stuff depending on the pattern of your shuffle.
    __m256i  shuffled = _mm256_shuffle_epi8(src, shuffle_control);

    // or if the pattern continues, and you're just leaving 2 bytes between every 2-byte group:
    shuffled = _mm256_cvtepu16_epi32(src);  // if src is a __m128i

    __m256i  blended = _mm256_blendv_epi8(shuffled, dst, shuffle_control);
    // blend dst elements we want to keep into the shuffled src result.
    return blended;
}

请注意 pshufb对于第二个 16 个字节，编号从 0 重新开始。 __m256i的两半可以不同，但​​他们不能从另一半读取元素。如果您需要在高车道中的位置从低车道获取字节，则需要更多的混洗+混合(例如包括 vinserti128 或 vperm2i128 ，或者可能是 vpermd 车道交叉双字混洗)来获得所有按某种顺序将您需要的字节放入一个 16 字节的组中。

(实际上 _mm256_shuffle_epi8 (PSHUFB) 忽略了 shuffle 索引中的第 4..6 位，所以写 17 与 1 相同，但非常具有误导性。它实际上是在做一个 %16 ，只要高位未设置。如果在 shuffle-control vector 中设置了高位，则将该元素归零。我们在这里不需要该功能；_mm256_blendv_epi8 不关心它正在替换的元素的旧值)

无论如何，这个简单的 2 指令示例仅在模式不继续时才有效。如果您在设计真正的洗牌时需要帮助，则必须提出更具体的问题。

顺便说一句，我注意到你的混合模式使用了 2 个新字节然后 2 跳过了 2 .如果这种情况继续下去，您可以使用 vpblendw _mm256_blend_epi16 而不是 blendv ，因为该指令在 Intel CPU 上仅以 1 uop 而不是 2 uop 运行。它还允许您使用 AVX512BW vpermw ，当前 Skylake-AVX512 CPU 中可用的 16 位 shuffle，而不是可能更慢的 AVX512VBMI vpermb .

或者实际上，它可能会让你使用 vpmovzxwd ( _mm256_cvtepu16_epi32 ) 将 16 位元素零扩展到 32 位，作为车道交叉洗牌。然后与 dst 混合.

关于c++ - 使用英特尔 AVX 通过掩码改组，我们在Stack Overflow上找到一个类似的问题： https://stackoverflow.com/questions/50098902/

英特ampcodeshuffle256c++ssesimdintrinsicsavx

有关c++ - 使用英特尔 AVX 通过掩码改组的更多相关文章

  1. ruby - 如何使用 Nokogiri 的 xpath 和 at_xpath 方法 - 2

    我正在学习如何使用Nokogiri，根据这段代码我遇到了一些问题:require'rubygems'require'mechanize'post_agent=WWW::Mechanize.newpost_page=post_agent.get('http://www.vbulletin.org/forum/showthread.php?t=230708')puts"\nabsolutepathwithtbodygivesnil"putspost_page.parser.xpath('/html/body/div/div/div/div/div/table/tbody/tr/td/div

  2. ruby - 使用 RubyZip 生成 ZIP 文件时设置压缩级别 - 2

    我有一个Ruby程序，它使用rubyzip压缩XML文件的目录树。gem。我的问题是文件开始变得很重，我想提高压缩级别，因为压缩时间不是问题。我在rubyzipdocumentation中找不到一种为创建的ZIP文件指定压缩级别的方法。有人知道如何更改此设置吗？是否有另一个允许指定压缩级别的Ruby库？ 最佳答案 这是我通过查看ruby​​zip内部创建的代码。level=Zlib::BEST_COMPRESSIONZip::ZipOutputStream.open(zip_file)do|zip|Dir.glob("**/*")d

  3. ruby - 为什么我可以在 Ruby 中使用 Object#send 访问私有(private)/ protected 方法？ - 2

    类classAprivatedeffooputs:fooendpublicdefbarputs:barendprivatedefzimputs:zimendprotecteddefdibputs:dibendendA的实例a=A.new测试a.foorescueputs:faila.barrescueputs:faila.zimrescueputs:faila.dibrescueputs:faila.gazrescueputs:fail测试输出failbarfailfailfail.发送测试[:foo,:bar,:zim,:dib,:gaz].each{|m|a.send(m)resc

  4. ruby-on-rails - 使用 Ruby on Rails 进行自动化测试 - 最佳实践 - 2

    很好奇，就使用ruby​​onrails自动化单元测试而言，你们正在做什么？您是否创建了一个脚本来在cron中运行rake作业并将结果邮寄给您？git中的预提交Hook？只是手动调用？我完全理解测试，但想知道在错误发生之前捕获错误的最佳实践是什么。让我们理所当然地认为测试本身是完美无缺的，并且可以正常工作。下一步是什么以确保他们在正确的时间将可能有害的结果传达给您？ 最佳答案 不确定您到底想听什么，但是有几个级别的自动代码库控制:在处理某项功能时，您可以使用类似autotest的内容获得关于哪些有效，哪些无效的即时反馈。要确保您的提

  5. ruby - 在 Ruby 中使用匿名模块 - 2

    假设我做了一个模块如下:m=Module.newdoclassCendend三个问题:除了对m的引用之外，还有什么方法可以访问C和m中的其他内容？我可以在创建匿名模块后为其命名吗(就像我输入“module...”一样)？如何在使用完匿名模块后将其删除，使其定义的常量不再存在？ 最佳答案 三个答案:是的，使用ObjectSpace.此代码使c引用你的类(class)C不引用m:c=nilObjectSpace.each_object{|obj|c=objif(Class===objandobj.name=~/::C$/)}当然这取决于

  6. ruby - 使用 ruby​​ 和 savon 的 SOAP 服务 - 2

    我正在尝试使用ruby​​和Savon来使用网络服务。测试服务为http://www.webservicex.net/WS/WSDetails.aspx?WSID=9&CATID=2require'rubygems'require'savon'client=Savon::Client.new"http://www.webservicex.net/stockquote.asmx?WSDL"client.get_quotedo|soap|soap.body={:symbol=>"AAPL"}end返回SOAP异常。检查soap信封，在我看来soap请求没有正确的命名空间。任何人都可以建议我

  7. python - 如何使用 Ruby 或 Python 创建一系列高音调和低音调的蜂鸣声？ - 2

    关闭。这个问题是opinion-based.它目前不接受答案。想要改进这个问题？更新问题，以便editingthispost可以用事实和引用来回答它.关闭4年前。Improvethisquestion我想在固定时间创建一系列低音和高音调的哔哔声。例如:在150毫秒时发出高音调的蜂鸣声在151毫秒时发出低音调的蜂鸣声200毫秒时发出低音调的蜂鸣声250毫秒的高音调蜂鸣声有没有办法在Ruby或Python中做到这一点？我真的不在乎输出编码是什么(.wav、.mp3、.ogg等等)，但我确实想创建一个输出文件。

  8. ruby-on-rails - 'compass watch' 是如何工作的/它是如何与 rails 一起使用的 - 2

    我在我的项目目录中完成了compasscreate.和compassinitrails。几个问题:我已将我的.sass文件放在public/stylesheets中。这是放置它们的正确位置吗？当我运行compasswatch时，它不会自动编译这些.sass文件。我必须手动指定文件:compasswatchpublic/stylesheets/myfile.sass等。如何让它自动运行？文件ie.css、print.css和screen.css已放在stylesheets/compiled。如何在编译后不让它们重新出现的情况下删除它们？我自己编译的.sass文件编译成compiled/t

  9. ruby - 使用 ruby​​ 将 HTML 转换为纯文本并维护结构/格式 - 2

    我想将html转换为纯文本。不过，我不想只删除标签，我想智能地保留尽可能多的格式。为插入换行符标签，检测段落并格式化它们等。输入非常简单，通常是格式良好的html(不是整个文档，只是一堆内容，通常没有anchor或图像)。我可以将几个正则表达式放在一起，让我达到80%，但我认为可能有一些现有的解决方案更智能。 最佳答案 首先，不要尝试为此使用正则表达式。很有可能你会想出一个脆弱/脆弱的解决方案，它会随着HTML的变化而崩溃，或者很难管理和维护。您可以使用Nokogiri快速解析HTML并提取文本:require'nokogiri'h

  10. ruby - 在 64 位 Snow Leopard 上使用 rvm、postgres 9.0、ruby 1.9.2-p136 安装 pg gem 时出现问题 - 2

    我想为Heroku构建一个Rails3应用程序。他们使用Postgres作为他们的数据库，所以我通过MacPorts安装了postgres9.0。现在我需要一个postgresgem并且共识是出于性能原因你想要pggem。但是我对我得到的错误感到非常困惑当我尝试在rvm下通过geminstall安装pg时。我已经非常明确地指定了所有postgres目录的位置可以找到但仍然无法完成安装:$envARCHFLAGS='-archx86_64'geminstallpg--\--with-pg-config=/opt/local/var/db/postgresql90/defaultdb/po

随机推荐