菜鸟教程小白 发表于 2022-12-12 23:11:53

ios - 在 iOS 上使用 NEON 乘积


                                            <p><p>即使我只为 <code>armv7</code> 进行编译，NEON 乘法累加内在函数似乎被分解为单独的乘法和加法。 </p>

<p>我在 Xcode 最新 4.5 的多个版本、iOS SDK 5 到 6 以及不同的优化设置(通过 Xcode 构建和直接通过命令行构建)都经历过这种情况。 </p>

<p>例如，构建和反汇编一些 <code>test.cpp</code> 包含</p>

<pre><code>#include &lt;arm_neon.h&gt;

float32x4_t test( float32x4_t a, float32x4_t b, float32x4_t c )
{
   float32x4_t result = a;
   result = vmlaq_f32( result, b, c );
   return result;
}
</code></pre>

<p>与</p>

<pre><code>clang++ -c -O3 -arch armv7 -o &#34;test.o&#34; test.cpp
otool -arch armv7 -tv test.o
</code></pre>

<p>结果</p>

<pre><code>test.o:
(__TEXT,__text) section
__Z4test19__simd128_float32_tS_S_:
00000000    f10d0910    add.w   r9, sp, #16 @ 0x10
00000004      46ec    mov ip, sp
00000006    ecdc2b04    vldmiaip, {d18-d19}
0000000a    ecd90b04    vldmiar9, {d16-d17}
0000000e    ff420df0    vmul.f32    q8, q9, q8
00000012    ec432b33    vmov    d19, r2, r3
00000016    ec410b32    vmov    d18, r0, r1
0000001a    ef400de2    vadd.f32    q8, q8, q9
0000001e    ec510b30    vmov    r0, r1, d16
00000022    ec532b31    vmov    r2, r3, d17
00000026      4770    bxlr
</code></pre>

<p>而不是 <code>vmla.f32</code> 的预期用途。 </p>

<p>请问我做错了什么？</p></p>
                                    <br><hr><h1><strong>Best Answer-推荐答案</ strong></h1><br>
                                            <p><p>这是一个错误或 llvm-clang 的优化。 armcc 或 gcc 会按照您的预期生成 vmla，但如果您阅读 <em>Cortex-A 系列程序员指南 v3</em>，它会说:</p>

<blockquote>
<blockquote>
    <p><strong>20.2.3 Scheduling</strong></p>
   
    <p>In some cases there can be a considerable latency, particularly VMLA multiply-accumulate (five cycles for an integer; seven cycles for a floating-point). Code using these instructions should be optimized to avoid trying to use the result value before it is ready, otherwise a stall will occur. Despite having a few cycles result latency, these instructions do fully pipeline so several
    operations can be in flight at once.</p>
</blockquote>
</blockquote>

<p>因此，llvm-clang 将 vmla 分离为乘法并累加以填充管道是有意义的。</p></p>
                                   
                                                <p style="font-size: 20px;">关于ios - 在 iOS 上使用 NEON 乘积，我们在Stack Overflow上找到一个类似的问题：
                                                        <a href="https://stackoverflow.com/questions/12932940/" rel="noreferrer noopener nofollow" style="color: red;">
                                                                https://stackoverflow.com/questions/12932940/
                                                        </a>
                                                </p>
                                       
页: [1]
查看完整版本: ios - 在 iOS 上使用 NEON 乘积