SSEインライン・チェック・ゼロ・フラグ

Question

インテルのSSE組み込み関数を使用してプロセッサのフラグ・レジスタをチェックすることが可能かどうか疑問に思っていましたか？例えば

：

int idx = _mm_cmpistri(mmrange, mmstr, 0x14); 
int zero = _mm_cmpistrz(mmrange, mmstr, 0x14); 

この例では、コンパイラは、単一の命令（pcmpistri）にこれら二つの組み込み関数を最適化することができ、フラグがジャンプ命令（jz）によって登録確認。

しかし、次の例にコンパイラが適切にコードを最適化するために管理していない：ここ

__m128i mmmask = _mm_cmpistrm(mmoldchar, mmstr, 0x40); 
int zero = _mm_cmpistrz(mmoldchar, mmstr, 0x40); 

は、コンパイラはpcmpistrmとpcmpistri命令を生成します。しかし、私の意見では、pcmpistrmはpcmistriと同じ方法でプロセッサのフラグレジスタにフラグを設定するので、2番目の命令は冗長です。

私の質問に戻るには、フラグレジスタを直接読み込む方法と、pcmpistrm命令だけを生成するようにコンパイラに指示する方法がありますか？

Answer 1

MSVCの最適化されていないバグのように見えますが、それは固有のものではありません。

#include <immintrin.h> 
__m128i foo(__m128i mmoldchar, __m128i mmstr) 
{  
    __m128i mmmask = _mm_cmpistrm(mmoldchar, mmstr, 0x40); 
    int zero = _mm_cmpistrz(mmoldchar, mmstr, 0x40); 
    if(zero) 
    return mmmask; 
    else 
    return _mm_setzero_si128(); 
} 

    ##gcc6.2 -O3 -march=nehalem 
    pcmpistrm  xmm0, xmm1, 64 
    je  .L5 
    pxor xmm0, xmm0 
    ret 
.L5: 
    ret 

OTOH、clang3.9はCSE、および用途に失敗します。

gcc6.2とicc17が正常にテスト関数に1 PCMPISTRMからの両方の結果を使用するには、私はzero結果の枝（on the Godbolt compiler explorer）と書きましたPCMPISTRI。

foo: 
    movdqa xmm2, xmm0 
    pcmpistri  xmm2, xmm1, 64 
    pxor xmm0, xmm0 
    jne  .LBB0_2 
    pcmpistrm  xmm2, xmm1, 64 
.LBB0_2: 
    ret 

---

Agner Fog's instruction tablesによると、PCMPISTRMが良いスループットが、高遅延を持っているので、待ち時間がボトルネックになっている場合は、並列に2を行うには、部屋の多くがあります注意してください。 __readflags()を使用するようなフープをジャンプすると、実際には悪化する可能性があります。

Answer 2

私自身が解決策を見つけました。

__readeflags()と呼ばれるフラグレジスタを読み取る機能があります。それはpushf（x64 plattformsのpushfq）命令をラップします。

__m128i mmmask = _mm_cmpistrm(mmoldchar, mmstr, 0x40); 
int zero = __readeflags() & 0x40; //0x40 is the mask for the zero flag (bit 6) 

このソリューションは最適ではありませんが、それはトリックを行います。

コードは次のようになります。