<div dir="ltr">You are correct that the initialization is unnecessary for the calculation of the result of the instruction.<div><br></div><div>It's zero in the IR because the intrinsic header file uses _mm256_undefined_si256() which is defined as zero for other reasons. See <a href="http://llvm.org/PR32176">llvm.org/PR32176</a>. We don't currently have a convenient way to put undef in the IR from C code.</div><div><br></div><div><div>#define _mm256_i32gather_epi32(m, i, s) __extension__ ({ \</div><div> (__m256i)__builtin_ia32_gatherd_d256((__v8si)_mm256_undefined_si256(), \</div><div> (int const *)(m), (__v8si)(__m256i)(i), \</div><div> (__v8si)_mm256_set1_epi32(-1), (s)); })</div></div><div><br></div><div>Now the backend could detect that mask is all 1s and remove the zero. But the backend knows one additional thing about the gather instructions. Even though the mask is all ones, the scheduler in the CPU doesn't know that until the gather instruction executes. That means the scheduler has to conservatively assume that the passthru input may be used by the instruction so the gather can't execute until the last writer of whatever register is chosen has executed and produced its result. Even though that result isn't going to be used by the gather. This is a false scheduling dependency. To break the dependency we emit an explicit zeroing with an xor which has special treatment in the CPU. The xor result will be considered ready without ever executing and the gather won't wait for it.</div><div><br></div><div>The backend will replace any non-zero or undef value with zero when it can prove the mask is all ones.</div><div><br></div><div>We could be smarter and try to find a register that hasn't been written in a while and use the zeroing as a last resort, but that's harder. We should maybe not emit the zero with -Os or -Oz either, but no one has complained about that yet.</div><div><br></div></div><div class="gmail_extra"><br clear="all"><div><div class="gmail_signature" data-smartmail="gmail_signature">~Craig</div></div>
<br><div class="gmail_quote">On Mon, Dec 18, 2017 at 4:52 PM, Jackson Davis via llvm-dev <span dir="ltr"><<a href="mailto:llvm-dev@lists.llvm.org" target="_blank">llvm-dev@lists.llvm.org</a>></span> wrote:<br><blockquote class="gmail_quote" style="margin:0 0 0 .8ex;border-left:1px #ccc solid;padding-left:1ex"><div dir="ltr"><div>Hi,<br><br></div>I've been looking into some basic vectorized code using <div><span style="color:rgb(0,0,0)"> _mm256_i32gather_epi32 for vpgatherdd. In a basic function I've been testing, I'm a little confused that it zeroes out the result before the gather (example: <a href="https://godbolt.org/g/zQzn56" target="_blank">https://godbolt.org/g/zQzn56</a>). Shouldn't this be unnecessary when the mask is not specified by the intrinsic (and therefor set for every element), in which case the resulting ymm register will be fully loaded? The IR seems to specify a pre-zeroed result if I'm understanding things correctly:<br></span></div><div><span style="color:rgb(0,0,0)"><br></span></div><div><br><div style="color:rgb(0,0,0);background-color:rgb(255,255,254);font-family:Fira Mono;font-weight:normal;font-size:14px;line-height:21px;white-space:pre-wrap"><div><span style="color:rgb(205,49,49)">%8</span><span style="color:rgb(0,0,0)"> </span><span style="color:rgb(205,49,49)">=</span><span style="color:rgb(0,0,0)"> </span><span style="color:rgb(0,0,255)">tail</span><span style="color:rgb(0,0,0)"> </span><span style="color:rgb(0,128,128)">call</span><span style="color:rgb(0,0,0)"> <</span><span style="color:rgb(9,136,90)">8</span><span style="color:rgb(0,0,0)"> </span><span style="color:rgb(0,128,128)">x</span><span style="color:rgb(0,0,0)"> </span><span style="color:rgb(0,128,128)">i32</span><span style="color:rgb(0,0,0)">> </span><span style="color:rgb(0,128,128)">@llvm.x86.avx2.gather.d.d.256</span><span style="color:rgb(0,0,0)">(<wbr><</span><span style="color:rgb(9,136,90)">8</span><span style="color:rgb(0,0,0)"> </span><span style="color:rgb(0,128,128)">x</span><span style="color:rgb(0,0,0)"> </span><span style="color:rgb(0,128,128)">i32</span><span style="color:rgb(0,0,0)">> </span><span style="color:rgb(0,128,128)">zeroinitializer</span><span style="color:rgb(0,0,0)">, </span><span style="color:rgb(0,128,128)">i8</span><span style="color:rgb(0,0,0)">* </span><span style="color:rgb(205,49,49)">%</span><span style="color:rgb(9,136,90)">1</span><span style="color:rgb(0,0,0)">, <</span><span style="color:rgb(9,136,90)">8</span><span style="color:rgb(0,0,0)"> </span><span style="color:rgb(0,128,128)">x</span><span style="color:rgb(0,0,0)"> </span><span style="color:rgb(0,128,128)">i32</span><span style="color:rgb(0,0,0)">> </span><span style="color:rgb(205,49,49)">%</span><span style="color:rgb(9,136,90)">7</span><span style="color:rgb(0,0,0)">, <</span><span style="color:rgb(9,136,90)">8</span><span style="color:rgb(0,0,0)"> </span><span style="color:rgb(0,128,128)">x</span><span style="color:rgb(0,0,0)"> </span><span style="color:rgb(0,128,128)">i32</span><span style="color:rgb(0,0,0)">> <</span><span style="color:rgb(0,128,128)">i32</span><span style="color:rgb(0,0,0)"> -</span><span style="color:rgb(9,136,90)">1</span><span style="color:rgb(0,0,0)">, </span><span style="color:rgb(0,128,128)">i32</span><span style="color:rgb(0,0,0)"> -</span><span style="color:rgb(9,136,90)">1</span><span style="color:rgb(0,0,0)">, </span><span style="color:rgb(0,128,128)">i32</span><span style="color:rgb(0,0,0)"> -</span><span style="color:rgb(9,136,90)">1</span><span style="color:rgb(0,0,0)">, </span><span style="color:rgb(0,128,128)">i32</span><span style="color:rgb(0,0,0)"> -</span><span style="color:rgb(9,136,90)">1</span><span style="color:rgb(0,0,0)">, </span><span style="color:rgb(0,128,128)">i32</span><span style="color:rgb(0,0,0)"> -</span><span style="color:rgb(9,136,90)">1</span><span style="color:rgb(0,0,0)">, </span><span style="color:rgb(0,128,128)">i32</span><span style="color:rgb(0,0,0)"> -</span><span style="color:rgb(9,136,90)">1</span><span style="color:rgb(0,0,0)">, </span><span style="color:rgb(0,128,128)">i32</span><span style="color:rgb(0,0,0)"> -</span><span style="color:rgb(9,136,90)">1</span><span style="color:rgb(0,0,0)">, </span><span style="color:rgb(0,128,128)">i32</span><span style="color:rgb(0,0,0)"> -</span><span style="color:rgb(9,136,90)">1</span><span style="color:rgb(0,0,0)">>, </span><span style="color:rgb(0,128,128)">i8</span><span style="color:rgb(0,0,0)"> </span><span style="color:rgb(9,136,90)">1</span><span style="color:rgb(0,0,0)">)</span></div></div><span style="color:rgb(0,0,0)"></span></div><div><span style="color:rgb(0,0,0)"><br></span></div><div><span style="color:rgb(0,0,0)">Am I correct in thinking this initialization is unnecessary here given than the mask is all -1? I'm not really concerned with the cost of the initialization as much as I am concerned that I don't fully understand the semantics of the instruction/intrinsic :)</span></div><div><span style="color:rgb(0,0,0)"><br></span></div><div><span style="color:rgb(0,0,0)">Thanks,</span></div><div><span style="color:rgb(0,0,0)">-Jackson<br></span></div></div>
<br>______________________________<wbr>_________________<br>
LLVM Developers mailing list<br>
<a href="mailto:llvm-dev@lists.llvm.org">llvm-dev@lists.llvm.org</a><br>
<a href="http://lists.llvm.org/cgi-bin/mailman/listinfo/llvm-dev" rel="noreferrer" target="_blank">http://lists.llvm.org/cgi-bin/<wbr>mailman/listinfo/llvm-dev</a><br>
<br></blockquote></div><br></div>