<p dir="ltr">Hi James, </p>
<p dir="ltr">I disagree with you completely on every point except that you need to write new tests. </p>
<p dir="ltr">There is absolutely, as I said in the thread where I noticed this for the x86 intrinsics, that you cannot supply this test up and test it in the front and the back end separately. If you believe this is impossible please let me know why, but clang and llvm are designed to be tested as I stated. As far as prior art, I can only apologize that I didn't see them before, I'm sure you know how hard it is to review everything. </p>
<p dir="ltr">Thanks</p>
<p dir="ltr">-eric<br>
</p>
<p dir="ltr"></p>
<p dir="ltr">On Tue, Dec 1, 2015, 3:44 AM James Molloy <<a href="mailto:james@jamesmolloy.co.uk">james@jamesmolloy.co.uk</a>> wrote:</p>
<blockquote><p dir="ltr">Hi Eric,<br></p>
<p dir="ltr">While I agree with you in principle, Alexandros has just pointed out to me that all the other NEON intrinsics have such -O3 tests, and thinking about it I do think they add value. They test the full-trip through the compiler and ensure that Clang and LLVM have matching ideas of the IR interface exposed by the intrinsics.<br></p>
<p dir="ltr">AIUI, Alexandros wrote LLVM backend tests in addition to these. It does look like there are no tests just checking Clang's IR output - I think these should indeed be written.<br></p>
<p dir="ltr">In summary, I agree with you that we need tests for both Clang and LLVM separately. However I also think the full-trip tests add significant value and wouldn't like to see them removed, and there's significant prior art in this area so if we did decide they needed to be gone, we'd need a good discussion on how to regain the testing coverage we'd lose.<br>
</p>
</blockquote>
<p dir="ltr"><br><br></p>
<blockquote><p dir="ltr"></p>
<p dir="ltr">Cheers,<br></p>
<p dir="ltr">James<br></p>
<p dir="ltr">On Sun, 29 Nov 2015 at 20:40 Eric Christopher via cfe-commits <<a href="mailto:cfe-commits@lists.llvm.org">cfe-commits@lists.llvm.org</a>> wrote:</p>
</blockquote>
<blockquote><blockquote><p dir="ltr">Hi,</p>
<p dir="ltr">This is entirely the wrong way to do these tests. They shouldn't depend on assembly output or optimization. Please split them onto frontend IR tests and backend assembly tests. </p>
<p dir="ltr">Thanks!<br></p>
<p dir="ltr">On Sun, Nov 29, 2015, 2:56 AM Alexandros Lamprineas via cfe-commits <<a href="mailto:cfe-commits@lists.llvm.org">cfe-commits@lists.llvm.org</a>> wrote:</p>
</blockquote>
</blockquote>
<blockquote><blockquote><blockquote><p dir="ltr">Author: alelab01<br>
Date: Sun Nov 29 04:53:28 2015<br>
New Revision: 254251</p>
<p dir="ltr">URL: <a href="http://llvm.org/viewvc/llvm-project?rev=254251&view=rev">http://</a><a href="http://llvm.org/viewvc/llvm-project?rev=254251&view=rev">llvm.org</a><a href="http://llvm.org/viewvc/llvm-project?rev=254251&view=rev">/</a><a href="http://llvm.org/viewvc/llvm-project?rev=254251&view=rev">viewvc</a><a href="http://llvm.org/viewvc/llvm-project?rev=254251&view=rev">/</a><a href="http://llvm.org/viewvc/llvm-project?rev=254251&view=rev">llvm-project</a><a href="http://llvm.org/viewvc/llvm-project?rev=254251&view=rev">?rev=254251&view=rev</a><br>
Log:<br>
ARM v8.1a adds Advanced SIMD instructions for Rounding Double Multiply<br>
Add/Subtract.</p>
<p dir="ltr">Add missing tests that accidentally were not committed in rL254250.</p>
<p dir="ltr">Differential Revision: <a href="http://reviews.llvm.org/D14982">http://</a><a href="http://reviews.llvm.org/D14982">reviews.llvm.org</a><a href="http://reviews.llvm.org/D14982">/D14982</a></p>
<p dir="ltr">Added:<br>
    cfe/trunk/test/CodeGen/aarch64-v8.1a-neon-intrinsics.c<br>
    cfe/trunk/test/CodeGen/arm-v8.1a-neon-intrinsics.c</p>
<p dir="ltr">Added: cfe/trunk/test/CodeGen/aarch64-v8.1a-neon-intrinsics.c<br>
URL: <a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/aarch64-v8.1a-neon-intrinsics.c?rev=254251&view=auto">http://</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/aarch64-v8.1a-neon-intrinsics.c?rev=254251&view=auto">llvm.org</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/aarch64-v8.1a-neon-intrinsics.c?rev=254251&view=auto">/</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/aarch64-v8.1a-neon-intrinsics.c?rev=254251&view=auto">viewvc</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/aarch64-v8.1a-neon-intrinsics.c?rev=254251&view=auto">/</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/aarch64-v8.1a-neon-intrinsics.c?rev=254251&view=auto">llvm-project</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/aarch64-v8.1a-neon-intrinsics.c?rev=254251&view=auto">/</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/aarch64-v8.1a-neon-intrinsics.c?rev=254251&view=auto">cfe</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/aarch64-v8.1a-neon-intrinsics.c?rev=254251&view=auto">/trunk/test/</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/aarch64-v8.1a-neon-intrinsics.c?rev=254251&view=auto">CodeGen</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/aarch64-v8.1a-neon-intrinsics.c?rev=254251&view=auto">/</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/aarch64-v8.1a-neon-intrinsics.c?rev=254251&view=auto">aarch64-v8.1a-neon-intrinsics.c</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/aarch64-v8.1a-neon-intrinsics.c?rev=254251&view=auto">?rev=254251&view=auto</a><br>
==============================================================================<br>
--- cfe/trunk/test/CodeGen/aarch64-v8.1a-neon-intrinsics.c (added)<br>
+++ cfe/trunk/test/CodeGen/aarch64-v8.1a-neon-intrinsics.c Sun Nov 29 04:53:28 2015<br>
@@ -0,0 +1,128 @@<br>
+// REQUIRES: aarch64-registered-target<br>
+<br>
+// RUN: %clang_cc1 -triple aarch64-linux-gnu -target-feature +neon \<br>
+// RUN:  -target-feature +v8.1a -O3 -S -o - %s \<br>
+// RUN:  | FileCheck %s --check-prefix=CHECK --check-prefix=CHECK-AARCH64<br>
+<br>
+ #include <arm_neon.h><br>
+<br>
+// CHECK-AARCH64-LABEL: test_vqrdmlah_laneq_s16<br>
+int16x4_t test_vqrdmlah_laneq_s16(int16x4_t a, int16x4_t b, int16x8_t v) {<br>
+// CHECK-AARCH64: sqrdmlah {{v[0-9]+}}.4h, {{v[0-9]+}}.4h, {{v[0-9]+}}.h[7]<br>
+  return vqrdmlah_laneq_s16(a, b, v, 7);<br>
+}<br>
+<br>
+// CHECK-AARCH64-LABEL: test_vqrdmlah_laneq_s32<br>
+int32x2_t test_vqrdmlah_laneq_s32(int32x2_t a, int32x2_t b, int32x4_t v) {<br>
+// CHECK-AARCH64: sqrdmlah {{v[0-9]+}}.2s, {{v[0-9]+}}.2s, {{v[0-9]+}}.s[3]<br>
+  return vqrdmlah_laneq_s32(a, b, v, 3);<br>
+}<br>
+<br>
+// CHECK-AARCH64-LABEL: test_vqrdmlahq_laneq_s16<br>
+int16x8_t test_vqrdmlahq_laneq_s16(int16x8_t a, int16x8_t b, int16x8_t v) {<br>
+// CHECK-AARCH64: sqrdmlah {{v[0-9]+}}.8h, {{v[0-9]+}}.8h, {{v[0-9]+}}.h[7]<br>
+  return vqrdmlahq_laneq_s16(a, b, v, 7);<br>
+}<br>
+<br>
+// CHECK-AARCH64-LABEL: test_vqrdmlahq_laneq_s32<br>
+int32x4_t test_vqrdmlahq_laneq_s32(int32x4_t a, int32x4_t b, int32x4_t v) {<br>
+// CHECK-AARCH64: sqrdmlah {{v[0-9]+}}.4s, {{v[0-9]+}}.4s, {{v[0-9]+}}.s[3]<br>
+  return vqrdmlahq_laneq_s32(a, b, v, 3);<br>
+}<br>
+<br>
+// CHECK-AARCH64-LABEL: test_vqrdmlahh_s16<br>
+int16_t test_vqrdmlahh_s16(int16_t a, int16_t b, int16_t c) {<br>
+// CHECK-AARCH64: sqrdmlah {{h[0-9]+|v[0-9]+.4h}}, {{h[0-9]+|v[0-9]+.4h}}, {{h[0-9]+|v[0-9]+.4h}}<br>
+  return vqrdmlahh_s16(a, b, c);<br>
+}<br>
+<br>
+// CHECK-AARCH64-LABEL: test_vqrdmlahs_s32<br>
+int32_t test_vqrdmlahs_s32(int32_t a, int32_t b, int32_t c) {<br>
+// CHECK-AARCH64: sqrdmlah {{s[0-9]+}}, {{s[0-9]+}}, {{s[0-9]+}}<br>
+  return vqrdmlahs_s32(a, b, c);<br>
+}<br>
+<br>
+// CHECK-AARCH64-LABEL: test_vqrdmlahh_lane_s16<br>
+int16_t test_vqrdmlahh_lane_s16(int16_t a, int16_t b, int16x4_t c) {<br>
+// CHECK-AARCH64: sqrdmlah {{h[0-9]+|v[0-9]+.4h}}, {{h[0-9]+|v[0-9]+.4h}}, {{v[0-9]+}}.h[3]<br>
+  return vqrdmlahh_lane_s16(a, b, c, 3);<br>
+}<br>
+<br>
+// CHECK-AARCH64-LABEL: test_vqrdmlahs_lane_s32<br>
+int32_t test_vqrdmlahs_lane_s32(int32_t a, int32_t b, int32x2_t c) {<br>
+// CHECK-AARCH64: sqrdmlah {{s[0-9]+}}, {{s[0-9]+}}, {{v[0-9]+}}.s[1]<br>
+  return vqrdmlahs_lane_s32(a, b, c, 1);<br>
+}<br>
+<br>
+// CHECK-AARCH64-LABEL: test_vqrdmlahh_laneq_s16<br>
+int16_t test_vqrdmlahh_laneq_s16(int16_t a, int16_t b, int16x8_t c) {<br>
+// CHECK-AARCH64: sqrdmlah {{h[0-9]+|v[0-9]+.4h}}, {{h[0-9]+|v[0-9]+.4h}}, {{v[0-9]+}}.h[7]<br>
+  return vqrdmlahh_laneq_s16(a, b, c, 7);<br>
+}<br>
+<br>
+// CHECK-AARCH64-LABEL: test_vqrdmlahs_laneq_s32<br>
+int32_t test_vqrdmlahs_laneq_s32(int32_t a, int32_t b, int32x4_t c) {<br>
+// CHECK-AARCH64: sqrdmlah {{s[0-9]+}}, {{s[0-9]+}}, {{v[0-9]+}}.s[3]<br>
+  return vqrdmlahs_laneq_s32(a, b, c, 3);<br>
+}<br>
+<br>
+// CHECK-AARCH64-LABEL: test_vqrdmlsh_laneq_s16<br>
+int16x4_t test_vqrdmlsh_laneq_s16(int16x4_t a, int16x4_t b, int16x8_t v) {<br>
+// CHECK-AARCH64: sqrdmlsh {{v[0-9]+}}.4h, {{v[0-9]+}}.4h, {{v[0-9]+}}.h[7]<br>
+  return vqrdmlsh_laneq_s16(a, b, v, 7);<br>
+}<br>
+<br>
+// CHECK-AARCH64-LABEL: test_vqrdmlsh_laneq_s32<br>
+int32x2_t test_vqrdmlsh_laneq_s32(int32x2_t a, int32x2_t b, int32x4_t v) {<br>
+// CHECK-AARCH64: sqrdmlsh {{v[0-9]+}}.2s, {{v[0-9]+}}.2s, {{v[0-9]+}}.s[3]<br>
+  return vqrdmlsh_laneq_s32(a, b, v, 3);<br>
+}<br>
+<br>
+// CHECK-AARCH64-LABEL: test_vqrdmlshq_laneq_s16<br>
+int16x8_t test_vqrdmlshq_laneq_s16(int16x8_t a, int16x8_t b, int16x8_t v) {<br>
+// CHECK-AARCH64: sqrdmlsh {{v[0-9]+}}.8h, {{v[0-9]+}}.8h, {{v[0-9]+}}.h[7]<br>
+  return vqrdmlshq_laneq_s16(a, b, v, 7);<br>
+}<br>
+<br>
+// CHECK-AARCH64-LABEL: test_vqrdmlshq_laneq_s32<br>
+int32x4_t test_vqrdmlshq_laneq_s32(int32x4_t a, int32x4_t b, int32x4_t v) {<br>
+// CHECK-AARCH64: sqrdmlsh {{v[0-9]+}}.4s, {{v[0-9]+}}.4s, {{v[0-9]+}}.s[3]<br>
+  return vqrdmlshq_laneq_s32(a, b, v, 3);<br>
+}<br>
+<br>
+// CHECK-AARCH64-LABEL: test_vqrdmlshh_s16<br>
+int16_t test_vqrdmlshh_s16(int16_t a, int16_t b, int16_t c) {<br>
+// CHECK-AARCH64: sqrdmlsh {{h[0-9]+|v[0-9]+.4h}}, {{h[0-9]+|v[0-9]+.4h}}, {{h[0-9]+|v[0-9]+.4h}}<br>
+  return vqrdmlshh_s16(a, b, c);<br>
+}<br>
+<br>
+// CHECK-AARCH64-LABEL: test_vqrdmlshs_s32<br>
+int32_t test_vqrdmlshs_s32(int32_t a, int32_t b, int32_t c) {<br>
+// CHECK-AARCH64: sqrdmlsh {{s[0-9]+}}, {{s[0-9]+}}, {{s[0-9]+}}<br>
+  return vqrdmlshs_s32(a, b, c);<br>
+}<br>
+<br>
+// CHECK-AARCH64-LABEL: test_vqrdmlshh_lane_s16<br>
+int16_t test_vqrdmlshh_lane_s16(int16_t a, int16_t b, int16x4_t c) {<br>
+// CHECK-AARCH64: sqrdmlsh {{h[0-9]+|v[0-9]+.4h}}, {{h[0-9]+|v[0-9]+.4h}}, {{v[0-9]+}}.h[3]<br>
+  return vqrdmlshh_lane_s16(a, b, c, 3);<br>
+}<br>
+<br>
+// CHECK-AARCH64-LABEL: test_vqrdmlshs_lane_s32<br>
+int32_t test_vqrdmlshs_lane_s32(int32_t a, int32_t b, int32x2_t c) {<br>
+// CHECK-AARCH64: sqrdmlsh {{s[0-9]+}}, {{s[0-9]+}}, {{v[0-9]+}}.s[1]<br>
+  return vqrdmlshs_lane_s32(a, b, c, 1);<br>
+}<br>
+<br>
+// CHECK-AARCH64-LABEL: test_vqrdmlshh_laneq_s16<br>
+int16_t test_vqrdmlshh_laneq_s16(int16_t a, int16_t b, int16x8_t c) {<br>
+// CHECK-AARCH64: sqrdmlsh {{h[0-9]+|v[0-9]+.4h}}, {{h[0-9]+|v[0-9]+.4h}}, {{v[0-9]+}}.h[7]<br>
+  return vqrdmlshh_laneq_s16(a, b, c, 7);<br>
+}<br>
+<br>
+// CHECK-AARCH64-LABEL: test_vqrdmlshs_laneq_s32<br>
+int32_t test_vqrdmlshs_laneq_s32(int32_t a, int32_t b, int32x4_t c) {<br>
+// CHECK-AARCH64: sqrdmlsh {{s[0-9]+}}, {{s[0-9]+}}, {{v[0-9]+}}.s[3]<br>
+  return vqrdmlshs_laneq_s32(a, b, c, 3);<br>
+}<br>
+</p>
<p dir="ltr">Added: cfe/trunk/test/CodeGen/arm-v8.1a-neon-intrinsics.c<br>
URL: <a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/arm-v8.1a-neon-intrinsics.c?rev=254251&view=auto">http://</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/arm-v8.1a-neon-intrinsics.c?rev=254251&view=auto">llvm.org</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/arm-v8.1a-neon-intrinsics.c?rev=254251&view=auto">/</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/arm-v8.1a-neon-intrinsics.c?rev=254251&view=auto">viewvc</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/arm-v8.1a-neon-intrinsics.c?rev=254251&view=auto">/</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/arm-v8.1a-neon-intrinsics.c?rev=254251&view=auto">llvm-project</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/arm-v8.1a-neon-intrinsics.c?rev=254251&view=auto">/</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/arm-v8.1a-neon-intrinsics.c?rev=254251&view=auto">cfe</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/arm-v8.1a-neon-intrinsics.c?rev=254251&view=auto">/trunk/test/</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/arm-v8.1a-neon-intrinsics.c?rev=254251&view=auto">CodeGen</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/arm-v8.1a-neon-intrinsics.c?rev=254251&view=auto">/</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/arm-v8.1a-neon-intrinsics.c?rev=254251&view=auto">arm-v8.1a-neon-intrinsics.c</a><a href="http://llvm.org/viewvc/llvm-project/cfe/trunk/test/CodeGen/arm-v8.1a-neon-intrinsics.c?rev=254251&view=auto">?rev=254251&view=auto</a><br>
==============================================================================<br>
--- cfe/trunk/test/CodeGen/arm-v8.1a-neon-intrinsics.c (added)<br>
+++ cfe/trunk/test/CodeGen/arm-v8.1a-neon-intrinsics.c Sun Nov 29 04:53:28 2015<br>
@@ -0,0 +1,121 @@<br>
+// RUN: %clang_cc1 -triple armv8.1a-linux-gnu -target-feature +neon \<br>
+// RUN:  -O3 -S -o - %s \<br>
+// RUN:  | FileCheck %s --check-prefix=CHECK --check-prefix=CHECK-ARM<br>
+// RUN: %clang_cc1 -triple aarch64-linux-gnu -target-feature +neon \<br>
+// RUN:  -target-feature +v8.1a -O3 -S -o - %s \<br>
+// RUN:  | FileCheck %s --check-prefix=CHECK --check-prefix=CHECK-AARCH64<br>
+<br>
+#include <arm_neon.h><br>
+<br>
+// CHECK-LABEL: test_vqrdmlah_s16<br>
+int16x4_t test_vqrdmlah_s16(int16x4_t a, int16x4_t b, int16x4_t c) {<br>
+// CHECK-ARM: vqrdmlah.s16 d{{[0-9]+}}, d{{[0-9]+}}, d{{[0-9]+}}<br>
+// CHECK-AARCH64: sqrdmlah {{v[0-9]+}}.4h, {{v[0-9]+}}.4h, {{v[0-9]+}}.4h<br>
+  return vqrdmlah_s16(a, b, c);<br>
+}<br>
+<br>
+// CHECK-LABEL: test_vqrdmlah_s32<br>
+int32x2_t test_vqrdmlah_s32(int32x2_t a, int32x2_t b, int32x2_t c) {<br>
+// CHECK-ARM: vqrdmlah.s32 d{{[0-9]+}}, d{{[0-9]+}}, d{{[0-9]+}}<br>
+// CHECK-AARCH64: sqrdmlah {{v[0-9]+}}.2s, {{v[0-9]+}}.2s, {{v[0-9]+}}.2s<br>
+  return vqrdmlah_s32(a, b, c);<br>
+}<br>
+<br>
+// CHECK-LABEL: test_vqrdmlahq_s16<br>
+int16x8_t test_vqrdmlahq_s16(int16x8_t a, int16x8_t b, int16x8_t c) {<br>
+// CHECK-ARM: vqrdmlah.s16 q{{[0-9]+}}, q{{[0-9]+}}, q{{[0-9]+}}<br>
+// CHECK-AARCH64: sqrdmlah {{v[0-9]+}}.8h, {{v[0-9]+}}.8h, {{v[0-9]+}}.8h<br>
+  return vqrdmlahq_s16(a, b, c);<br>
+}<br>
+<br>
+// CHECK-LABEL: test_vqrdmlahq_s32<br>
+int32x4_t test_vqrdmlahq_s32(int32x4_t a, int32x4_t b, int32x4_t c) {<br>
+// CHECK-ARM: vqrdmlah.s32 q{{[0-9]+}}, q{{[0-9]+}}, q{{[0-9]+}}<br>
+// CHECK-AARCH64: sqrdmlah {{v[0-9]+}}.4s, {{v[0-9]+}}.4s, {{v[0-9]+}}.4s<br>
+  return vqrdmlahq_s32(a, b, c);<br>
+}<br>
+<br>
+// CHECK-LABEL: test_vqrdmlah_lane_s16<br>
+int16x4_t test_vqrdmlah_lane_s16(int16x4_t a, int16x4_t b, int16x4_t c) {<br>
+// CHECK-ARM: vqrdmlah.s16 d{{[0-9]+}}, d{{[0-9]+}}, d{{[0-9]+}}[3]<br>
+// CHECK-AARCH64: sqrdmlah {{v[0-9]+}}.4h, {{v[0-9]+}}.4h, {{v[0-9]+}}.h[3]<br>
+  return vqrdmlah_lane_s16(a, b, c, 3);<br>
+}<br>
+<br>
+// CHECK-LABEL: test_vqrdmlah_lane_s32<br>
+int32x2_t test_vqrdmlah_lane_s32(int32x2_t a, int32x2_t b, int32x2_t c) {<br>
+// CHECK-ARM: vqrdmlah.s32 d{{[0-9]+}}, d{{[0-9]+}}, d{{[0-9]+}}[1]<br>
+// CHECK-AARCH64: sqrdmlah {{v[0-9]+}}.2s, {{v[0-9]+}}.2s, {{v[0-9]+}}.s[1]<br>
+  return vqrdmlah_lane_s32(a, b, c, 1);<br>
+}<br>
+<br>
+// CHECK-LABEL: test_vqrdmlahq_lane_s16<br>
+int16x8_t test_vqrdmlahq_lane_s16(int16x8_t a, int16x8_t b, int16x4_t c) {<br>
+// CHECK-ARM: vqrdmlah.s16 q{{[0-9]+}}, q{{[0-9]+}}, d{{[0-9]+}}[3]<br>
+// CHECK-AARCH64: sqrdmlah {{v[0-9]+}}.8h, {{v[0-9]+}}.8h, {{v[0-9]+}}.h[3]<br>
+  return vqrdmlahq_lane_s16(a, b, c, 3);<br>
+}<br>
+<br>
+// CHECK-LABEL: test_vqrdmlahq_lane_s32<br>
+int32x4_t test_vqrdmlahq_lane_s32(int32x4_t a, int32x4_t b, int32x2_t c) {<br>
+// CHECK-ARM: vqrdmlah.s32 q{{[0-9]+}}, q{{[0-9]+}}, d{{[0-9]+}}[1]<br>
+// CHECK-AARCH64: sqrdmlah {{v[0-9]+}}.4s, {{v[0-9]+}}.4s, {{v[0-9]+}}.s[1]<br>
+  return vqrdmlahq_lane_s32(a, b, c, 1);<br>
+}<br>
+<br>
+// CHECK-LABEL: test_vqrdmlsh_s16<br>
+int16x4_t test_vqrdmlsh_s16(int16x4_t a, int16x4_t b, int16x4_t c) {<br>
+// CHECK-ARM: vqrdmlsh.s16 d{{[0-9]+}}, d{{[0-9]+}}, d{{[0-9]+}}<br>
+// CHECK-AARCH64: sqrdmlsh {{v[0-9]+}}.4h, {{v[0-9]+}}.4h, {{v[0-9]+}}.4h<br>
+  return vqrdmlsh_s16(a, b, c);<br>
+}<br>
+<br>
+// CHECK-LABEL: test_vqrdmlsh_s32<br>
+int32x2_t test_vqrdmlsh_s32(int32x2_t a, int32x2_t b, int32x2_t c) {<br>
+// CHECK-ARM: vqrdmlsh.s32 d{{[0-9]+}}, d{{[0-9]+}}, d{{[0-9]+}}<br>
+// CHECK-AARCH64: sqrdmlsh {{v[0-9]+}}.2s, {{v[0-9]+}}.2s, {{v[0-9]+}}.2s<br>
+  return vqrdmlsh_s32(a, b, c);<br>
+}<br>
+<br>
+// CHECK-LABEL: test_vqrdmlshq_s16<br>
+int16x8_t test_vqrdmlshq_s16(int16x8_t a, int16x8_t b, int16x8_t c) {<br>
+// CHECK-ARM: vqrdmlsh.s16 q{{[0-9]+}}, q{{[0-9]+}}, q{{[0-9]+}}<br>
+// CHECK-AARCH64: sqrdmlsh {{v[0-9]+}}.8h, {{v[0-9]+}}.8h, {{v[0-9]+}}.8h<br>
+  return vqrdmlshq_s16(a, b, c);<br>
+}<br>
+<br>
+// CHECK-LABEL: test_vqrdmlshq_s32<br>
+int32x4_t test_vqrdmlshq_s32(int32x4_t a, int32x4_t b, int32x4_t c) {<br>
+// CHECK-ARM: vqrdmlsh.s32 q{{[0-9]+}}, q{{[0-9]+}}, q{{[0-9]+}}<br>
+// CHECK-AARCH64: sqrdmlsh {{v[0-9]+}}.4s, {{v[0-9]+}}.4s, {{v[0-9]+}}.4s<br>
+  return vqrdmlshq_s32(a, b, c);<br>
+}<br>
+<br>
+// CHECK-LABEL: test_vqrdmlsh_lane_s16<br>
+int16x4_t test_vqrdmlsh_lane_s16(int16x4_t a, int16x4_t b, int16x4_t c) {<br>
+// CHECK-ARM: vqrdmlsh.s16 d{{[0-9]+}}, d{{[0-9]+}}, d{{[0-9]+}}[3]<br>
+// CHECK-AARCH64: sqrdmlsh {{v[0-9]+}}.4h, {{v[0-9]+}}.4h, {{v[0-9]+}}.h[3]<br>
+  return vqrdmlsh_lane_s16(a, b, c, 3);<br>
+}<br>
+<br>
+// CHECK-LABEL: test_vqrdmlsh_lane_s32<br>
+int32x2_t test_vqrdmlsh_lane_s32(int32x2_t a, int32x2_t b, int32x2_t c) {<br>
+// CHECK-ARM: vqrdmlsh.s32 d{{[0-9]+}}, d{{[0-9]+}}, d{{[0-9]+}}[1]<br>
+// CHECK-AARCH64: sqrdmlsh {{v[0-9]+}}.2s, {{v[0-9]+}}.2s, {{v[0-9]+}}.s[1]<br>
+  return vqrdmlsh_lane_s32(a, b, c, 1);<br>
+}<br>
+<br>
+// CHECK-LABEL: test_vqrdmlshq_lane_s16<br>
+int16x8_t test_vqrdmlshq_lane_s16(int16x8_t a, int16x8_t b, int16x4_t c) {<br>
+// CHECK-ARM: vqrdmlsh.s16 q{{[0-9]+}}, q{{[0-9]+}}, d{{[0-9]+}}[3]<br>
+// CHECK-AARCH64: sqrdmlsh {{v[0-9]+}}.8h, {{v[0-9]+}}.8h, {{v[0-9]+}}.h[3]<br>
+  return vqrdmlshq_lane_s16(a, b, c, 3);<br>
+}<br>
+<br>
+// CHECK-LABEL: test_vqrdmlshq_lane_s32<br>
+int32x4_t test_vqrdmlshq_lane_s32(int32x4_t a, int32x4_t b, int32x2_t c) {<br>
+// CHECK-ARM: vqrdmlsh.s32 q{{[0-9]+}}, q{{[0-9]+}}, d{{[0-9]+}}[1]<br>
+// CHECK-AARCH64: sqrdmlsh {{v[0-9]+}}.4s, {{v[0-9]+}}.4s, {{v[0-9]+}}.s[1]<br>
+  return vqrdmlshq_lane_s32(a, b, c, 1);<br>
+}<br>
+<br></p>
<p dir="ltr">_______________________________________________<br>
cfe-commits mailing list<br>
<a href="mailto:cfe-commits@lists.llvm.org">cfe-commits@lists.llvm.org</a><br>
<a href="http://lists.llvm.org/cgi-bin/mailman/listinfo/cfe-commits">http://</a><a href="http://lists.llvm.org/cgi-bin/mailman/listinfo/cfe-commits">lists.llvm.org</a><a href="http://lists.llvm.org/cgi-bin/mailman/listinfo/cfe-commits">/</a><a href="http://lists.llvm.org/cgi-bin/mailman/listinfo/cfe-commits">cgi-bin</a><a href="http://lists.llvm.org/cgi-bin/mailman/listinfo/cfe-commits">/mailman/</a><a href="http://lists.llvm.org/cgi-bin/mailman/listinfo/cfe-commits">listinfo</a><a href="http://lists.llvm.org/cgi-bin/mailman/listinfo/cfe-commits">/</a><a href="http://lists.llvm.org/cgi-bin/mailman/listinfo/cfe-commits">cfe-commits</a><br>
</p>
</blockquote>
</blockquote>
</blockquote>
<blockquote><blockquote><p dir="ltr"><br>
_______________________________________________<br>
cfe-commits mailing list<br>
<a href="mailto:cfe-commits@lists.llvm.org">cfe-commits@lists.llvm.org</a><br>
<a href="http://lists.llvm.org/cgi-bin/mailman/listinfo/cfe-commits">http://</a><a href="http://lists.llvm.org/cgi-bin/mailman/listinfo/cfe-commits">lists.llvm.org</a><a href="http://lists.llvm.org/cgi-bin/mailman/listinfo/cfe-commits">/</a><a href="http://lists.llvm.org/cgi-bin/mailman/listinfo/cfe-commits">cgi-bin</a><a href="http://lists.llvm.org/cgi-bin/mailman/listinfo/cfe-commits">/mailman/</a><a href="http://lists.llvm.org/cgi-bin/mailman/listinfo/cfe-commits">listinfo</a><a href="http://lists.llvm.org/cgi-bin/mailman/listinfo/cfe-commits">/</a><a href="http://lists.llvm.org/cgi-bin/mailman/listinfo/cfe-commits">cfe-commits</a><br>
</p>
</blockquote>
</blockquote>
<p dir="ltr"><br>
</p>