Raspberry Pi 2 NEONインラインアセンブリ命令が動作しない

Question

RPi 2プロセッサがNEON命令をサポートしていることを発見したので、古いコードをより速く実行しようとしていました。だから私はこのコードを書いた：

__asm__ __volatile__(
    "vld1.8 {%%d2, %%d3}, [%1];" 
    "vld1.8 {%%d4, %%d5}, [%2];" 
    "vaba.u8 %%q0, %%q1, %%q2;" 
    "vst1.64 %%d0, [%0];" 
    : "=r" (address_sad_intermediary) 
    : "r" (address_big_pic), "r" (address_small_pic) 
    : 
); 

次にCにメイン悲しい変数はsad_intermediaryと加算されます。

主な目標は、big_picからq1レジスタに16B、small_picからq2レジスタに16Bをロードし、SADをq0に計算し、次にq0から下位8Bをロードします。中間変数。問題は、結果として得られる悲しみがゼロであることです。

私は-std = c99を-pthread -O3 -Wall -lm -march =のARMv7-A -mfpu =ネオンvfpv4ハード= -mfloat-ABIオプションでGCC 4.9.2を使用しています。

コードに問題はありませんか？ありがとう。

Answer 1

q0に何もロードしないので、vabaは、初期化されていないレジスタに絶対差を加えています。また、あなたが変更しているレジスタを宣言していないようです。

私はそれがあなたの問題の原因であるかどうかはわかりません。なぜなら、私はインラインアセンブリではあまり役に立ちませんからです。あなたはおそらくこのようなもののためにインラインアセンブリを使用すべきではありません。 intrinsicsを使用すると、コンパイラはコードを最適化する能力が向上します。このような何か：

#include <arm_neon.h> 

... 
uint8x8_t s = vld1_u8(address_sad_intermediary); 
s = vaba_u8(s, vld1_u8(address_big_pic), vld1_u8(address_small_pic)); 
vst1_u8(address_sad_intermediary, s); 

（あなただけのコードで8つのバイトを保存するので、このコードはわずか8つのバイトで動作することに注意してください）