| // REQUIRES: aarch64-registered-target |
| // RUN: %clang_cc1 -triple arm64-none-linux-gnu -target-feature +neon \ |
| // RUN: -ffp-contract=fast -S -O3 -o - %s | FileCheck %s |
| |
| // Test new aarch64 intrinsics and types |
| |
| #include <arm_neon.h> |
| |
| int8x8_t test_vtbl1_s8(int8x8_t a, int8x8_t b) { |
| // CHECK-LABEL: test_vtbl1_s8 |
| return vtbl1_s8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| int8x8_t test_vqtbl1_s8(int8x16_t a, int8x8_t b) { |
| // CHECK-LABEL: test_vqtbl1_s8 |
| return vqtbl1_s8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| int8x8_t test_vtbl2_s8(int8x8x2_t a, int8x8_t b) { |
| // CHECK-LABEL: test_vtbl2_s8 |
| return vtbl2_s8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| int8x8_t test_vqtbl2_s8(int8x16x2_t a, int8x8_t b) { |
| // CHECK-LABEL: test_vqtbl2_s8 |
| return vqtbl2_s8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| int8x8_t test_vtbl3_s8(int8x8x3_t a, int8x8_t b) { |
| // CHECK-LABEL: test_vtbl3_s8 |
| return vtbl3_s8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| int8x8_t test_vqtbl3_s8(int8x16x3_t a, int8x8_t b) { |
| // CHECK-LABEL: test_vqtbl3_s8 |
| return vqtbl3_s8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| int8x8_t test_vtbl4_s8(int8x8x4_t a, int8x8_t b) { |
| // CHECK-LABEL: test_vtbl4_s8 |
| return vtbl4_s8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| int8x8_t test_vqtbl4_s8(int8x16x4_t a, int8x8_t b) { |
| // CHECK-LABEL: test_vqtbl4_s8 |
| return vqtbl4_s8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| int8x16_t test_vqtbl1q_s8(int8x16_t a, int8x16_t b) { |
| // CHECK-LABEL: test_vqtbl1q_s8 |
| return vqtbl1q_s8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| int8x16_t test_vqtbl2q_s8(int8x16x2_t a, int8x16_t b) { |
| // CHECK-LABEL: test_vqtbl2q_s8 |
| return vqtbl2q_s8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| int8x16_t test_vqtbl3q_s8(int8x16x3_t a, int8x16_t b) { |
| // CHECK-LABEL: test_vqtbl3q_s8 |
| return vqtbl3q_s8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| int8x16_t test_vqtbl4q_s8(int8x16x4_t a, int8x16_t b) { |
| // CHECK-LABEL: test_vqtbl4q_s8 |
| return vqtbl4q_s8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| int8x8_t test_vtbx1_s8(int8x8_t a, int8x8_t b, int8x8_t c) { |
| // CHECK-LABEL: test_vtbx1_s8 |
| return vtbx1_s8(a, b, c); |
| // CHECK: movi {{v[0-9]+.8b|d[0-9]+}}, #0 |
| // CHECK: ins {{v[0-9]+}}.d[1], {{v[0-9]+}}.d[0] |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| // CHECK: cmhs {{v[0-9]+}}.8b, {{v[0-9]+}}.8b, {{v[0-9]+}}.8b |
| // CHECK: bsl {{v[0-9]+}}.8b, {{v[0-9]+}}.8b, {{v[0-9]+}}.8b |
| } |
| |
| int8x8_t test_vtbx2_s8(int8x8_t a, int8x8x2_t b, int8x8_t c) { |
| // CHECK-LABEL: test_vtbx2_s8 |
| return vtbx2_s8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| int8x8_t test_vtbx3_s8(int8x8_t a, int8x8x3_t b, int8x8_t c) { |
| // CHECK-LABEL: test_vtbx3_s8 |
| return vtbx3_s8(a, b, c); |
| // CHECK: movi {{v[0-9]+.8b|d[0-9]+}}, #0 |
| // CHECK: ins {{v[0-9]+}}.d[1], {{v[0-9]+}}.d[0] |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| // CHECK: cmhs {{v[0-9]+}}.8b, {{v[0-9]+}}.8b, {{v[0-9]+}}.8b |
| // CHECK: bsl {{v[0-9]+}}.8b, {{v[0-9]+}}.8b, {{v[0-9]+}}.8b |
| } |
| |
| int8x8_t test_vtbx4_s8(int8x8_t a, int8x8x4_t b, int8x8_t c) { |
| // CHECK-LABEL: test_vtbx4_s8 |
| return vtbx4_s8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| int8x8_t test_vqtbx1_s8(int8x8_t a, int8x16_t b, int8x8_t c) { |
| // CHECK-LABEL: test_vqtbx1_s8 |
| return vqtbx1_s8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| int8x8_t test_vqtbx2_s8(int8x8_t a, int8x16x2_t b, int8x8_t c) { |
| // CHECK-LABEL: test_vqtbx2_s8 |
| return vqtbx2_s8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| int8x8_t test_vqtbx3_s8(int8x8_t a, int8x16x3_t b, int8x8_t c) { |
| // CHECK-LABEL: test_vqtbx3_s8 |
| return vqtbx3_s8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| int8x8_t test_vqtbx4_s8(int8x8_t a, int8x16x4_t b, int8x8_t c) { |
| // CHECK-LABEL: test_vqtbx4_s8 |
| return vqtbx4_s8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| int8x16_t test_vqtbx1q_s8(int8x16_t a, int8x16_t b, int8x16_t c) { |
| // CHECK-LABEL: test_vqtbx1q_s8 |
| return vqtbx1q_s8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| int8x16_t test_vqtbx2q_s8(int8x16_t a, int8x16x2_t b, int8x16_t c) { |
| // CHECK-LABEL: test_vqtbx2q_s8 |
| return vqtbx2q_s8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| int8x16_t test_vqtbx3q_s8(int8x16_t a, int8x16x3_t b, int8x16_t c) { |
| // CHECK-LABEL: test_vqtbx3q_s8 |
| return vqtbx3q_s8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| int8x16_t test_vqtbx4q_s8(int8x16_t a, int8x16x4_t b, int8x16_t c) { |
| // CHECK-LABEL: test_vqtbx4q_s8 |
| return vqtbx4q_s8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| uint8x8_t test_vtbl1_u8(uint8x8_t a, uint8x8_t b) { |
| // CHECK-LABEL: test_vtbl1_u8 |
| return vtbl1_u8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| uint8x8_t test_vqtbl1_u8(uint8x16_t a, uint8x8_t b) { |
| // CHECK-LABEL: test_vqtbl1_u8 |
| return vqtbl1_u8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| uint8x8_t test_vtbl2_u8(uint8x8x2_t a, uint8x8_t b) { |
| // CHECK-LABEL: test_vtbl2_u8 |
| return vtbl2_u8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| uint8x8_t test_vqtbl2_u8(uint8x16x2_t a, uint8x8_t b) { |
| // CHECK-LABEL: test_vqtbl2_u8 |
| return vqtbl2_u8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| uint8x8_t test_vtbl3_u8(uint8x8x3_t a, uint8x8_t b) { |
| // CHECK-LABEL: test_vtbl3_u8 |
| return vtbl3_u8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| uint8x8_t test_vqtbl3_u8(uint8x16x3_t a, uint8x8_t b) { |
| // CHECK-LABEL: test_vqtbl3_u8 |
| return vqtbl3_u8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| uint8x8_t test_vtbl4_u8(uint8x8x4_t a, uint8x8_t b) { |
| // CHECK-LABEL: test_vtbl4_u8 |
| return vtbl4_u8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| uint8x8_t test_vqtbl4_u8(uint8x16x4_t a, uint8x8_t b) { |
| // CHECK-LABEL: test_vqtbl4_u8 |
| return vqtbl4_u8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| uint8x16_t test_vqtbl1q_u8(uint8x16_t a, uint8x16_t b) { |
| // CHECK-LABEL: test_vqtbl1q_u8 |
| return vqtbl1q_u8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| uint8x16_t test_vqtbl2q_u8(uint8x16x2_t a, uint8x16_t b) { |
| // CHECK-LABEL: test_vqtbl2q_u8 |
| return vqtbl2q_u8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| uint8x16_t test_vqtbl3q_u8(uint8x16x3_t a, uint8x16_t b) { |
| // CHECK-LABEL: test_vqtbl3q_u8 |
| return vqtbl3q_u8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| uint8x16_t test_vqtbl4q_u8(uint8x16x4_t a, uint8x16_t b) { |
| // CHECK-LABEL: test_vqtbl4q_u8 |
| return vqtbl4q_u8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| uint8x8_t test_vtbx1_u8(uint8x8_t a, uint8x8_t b, uint8x8_t c) { |
| // CHECK-LABEL: test_vtbx1_u8 |
| return vtbx1_u8(a, b, c); |
| // CHECK: movi {{v[0-9]+.8b|d[0-9]+}}, #0 |
| // CHECK: ins {{v[0-9]+}}.d[1], {{v[0-9]+}}.d[0] |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| // CHECK: cmhs {{v[0-9]+}}.8b, {{v[0-9]+}}.8b, {{v[0-9]+}}.8b |
| // CHECK: bsl {{v[0-9]+}}.8b, {{v[0-9]+}}.8b, {{v[0-9]+}}.8b |
| } |
| |
| uint8x8_t test_vtbx2_u8(uint8x8_t a, uint8x8x2_t b, uint8x8_t c) { |
| // CHECK-LABEL: test_vtbx2_u8 |
| return vtbx2_u8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| uint8x8_t test_vtbx3_u8(uint8x8_t a, uint8x8x3_t b, uint8x8_t c) { |
| // CHECK-LABEL: test_vtbx3_u8 |
| return vtbx3_u8(a, b, c); |
| // CHECK: movi {{v[0-9]+.8b|d[0-9]+}}, #0 |
| // CHECK: ins {{v[0-9]+}}.d[1], {{v[0-9]+}}.d[0] |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| // CHECK: cmhs {{v[0-9]+}}.8b, {{v[0-9]+}}.8b, {{v[0-9]+}}.8b |
| // CHECK: bsl {{v[0-9]+}}.8b, {{v[0-9]+}}.8b, {{v[0-9]+}}.8b |
| } |
| |
| uint8x8_t test_vtbx4_u8(uint8x8_t a, uint8x8x4_t b, uint8x8_t c) { |
| // CHECK-LABEL: test_vtbx4_u8 |
| return vtbx4_u8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| uint8x8_t test_vqtbx1_u8(uint8x8_t a, uint8x16_t b, uint8x8_t c) { |
| // CHECK-LABEL: test_vqtbx1_u8 |
| return vqtbx1_u8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| uint8x8_t test_vqtbx2_u8(uint8x8_t a, uint8x16x2_t b, uint8x8_t c) { |
| // CHECK-LABEL: test_vqtbx2_u8 |
| return vqtbx2_u8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| uint8x8_t test_vqtbx3_u8(uint8x8_t a, uint8x16x3_t b, uint8x8_t c) { |
| // CHECK-LABEL: test_vqtbx3_u8 |
| return vqtbx3_u8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| uint8x8_t test_vqtbx4_u8(uint8x8_t a, uint8x16x4_t b, uint8x8_t c) { |
| // CHECK-LABEL: test_vqtbx4_u8 |
| return vqtbx4_u8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| uint8x16_t test_vqtbx1q_u8(uint8x16_t a, uint8x16_t b, uint8x16_t c) { |
| // CHECK-LABEL: test_vqtbx1q_u8 |
| return vqtbx1q_u8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| uint8x16_t test_vqtbx2q_u8(uint8x16_t a, uint8x16x2_t b, uint8x16_t c) { |
| // CHECK-LABEL: test_vqtbx2q_u8 |
| return vqtbx2q_u8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| uint8x16_t test_vqtbx3q_u8(uint8x16_t a, uint8x16x3_t b, uint8x16_t c) { |
| // CHECK-LABEL: test_vqtbx3q_u8 |
| return vqtbx3q_u8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| uint8x16_t test_vqtbx4q_u8(uint8x16_t a, uint8x16x4_t b, uint8x16_t c) { |
| // CHECK-LABEL: test_vqtbx4q_u8 |
| return vqtbx4q_u8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| poly8x8_t test_vtbl1_p8(poly8x8_t a, uint8x8_t b) { |
| // CHECK-LABEL: test_vtbl1_p8 |
| return vtbl1_p8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| poly8x8_t test_vqtbl1_p8(poly8x16_t a, uint8x8_t b) { |
| // CHECK-LABEL: test_vqtbl1_p8 |
| return vqtbl1_p8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| poly8x8_t test_vtbl2_p8(poly8x8x2_t a, uint8x8_t b) { |
| // CHECK-LABEL: test_vtbl2_p8 |
| return vtbl2_p8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| poly8x8_t test_vqtbl2_p8(poly8x16x2_t a, uint8x8_t b) { |
| // CHECK-LABEL: test_vqtbl2_p8 |
| return vqtbl2_p8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| poly8x8_t test_vtbl3_p8(poly8x8x3_t a, uint8x8_t b) { |
| // CHECK-LABEL: test_vtbl3_p8 |
| return vtbl3_p8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| poly8x8_t test_vqtbl3_p8(poly8x16x3_t a, uint8x8_t b) { |
| // CHECK-LABEL: test_vqtbl3_p8 |
| return vqtbl3_p8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| poly8x8_t test_vtbl4_p8(poly8x8x4_t a, uint8x8_t b) { |
| // CHECK-LABEL: test_vtbl4_p8 |
| return vtbl4_p8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| poly8x8_t test_vqtbl4_p8(poly8x16x4_t a, uint8x8_t b) { |
| // CHECK-LABEL: test_vqtbl4_p8 |
| return vqtbl4_p8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| poly8x16_t test_vqtbl1q_p8(poly8x16_t a, uint8x16_t b) { |
| // CHECK-LABEL: test_vqtbl1q_p8 |
| return vqtbl1q_p8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| poly8x16_t test_vqtbl2q_p8(poly8x16x2_t a, uint8x16_t b) { |
| // CHECK-LABEL: test_vqtbl2q_p8 |
| return vqtbl2q_p8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| poly8x16_t test_vqtbl3q_p8(poly8x16x3_t a, uint8x16_t b) { |
| // CHECK-LABEL: test_vqtbl3q_p8 |
| return vqtbl3q_p8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| poly8x16_t test_vqtbl4q_p8(poly8x16x4_t a, uint8x16_t b) { |
| // CHECK-LABEL: test_vqtbl4q_p8 |
| return vqtbl4q_p8(a, b); |
| // CHECK: tbl {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| poly8x8_t test_vtbx1_p8(poly8x8_t a, poly8x8_t b, uint8x8_t c) { |
| // CHECK-LABEL: test_vtbx1_p8 |
| return vtbx1_p8(a, b, c); |
| // CHECK: movi {{v[0-9]+.8b|d[0-9]+}}, #0 |
| // CHECK: ins {{v[0-9]+}}.d[1], {{v[0-9]+}}.d[0] |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| // CHECK: cmhs {{v[0-9]+}}.8b, {{v[0-9]+}}.8b, {{v[0-9]+}}.8b |
| // CHECK: bsl {{v[0-9]+}}.8b, {{v[0-9]+}}.8b, {{v[0-9]+}}.8b |
| } |
| |
| poly8x8_t test_vtbx2_p8(poly8x8_t a, poly8x8x2_t b, uint8x8_t c) { |
| // CHECK-LABEL: test_vtbx2_p8 |
| return vtbx2_p8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| poly8x8_t test_vtbx3_p8(poly8x8_t a, poly8x8x3_t b, uint8x8_t c) { |
| // CHECK-LABEL: test_vtbx3_p8 |
| return vtbx3_p8(a, b, c); |
| // CHECK: movi {{v[0-9]+.8b|d[0-9]+}}, #0 |
| // CHECK: ins {{v[0-9]+}}.d[1], {{v[0-9]+}}.d[0] |
| // CHECK: tbl {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| // CHECK: cmhs {{v[0-9]+}}.8b, {{v[0-9]+}}.8b, {{v[0-9]+}}.8b |
| // CHECK: bsl {{v[0-9]+}}.8b, {{v[0-9]+}}.8b, {{v[0-9]+}}.8b |
| } |
| |
| poly8x8_t test_vtbx4_p8(poly8x8_t a, poly8x8x4_t b, uint8x8_t c) { |
| // CHECK-LABEL: test_vtbx4_p8 |
| return vtbx4_p8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| poly8x8_t test_vqtbx1_p8(poly8x8_t a, uint8x16_t b, uint8x8_t c) { |
| // CHECK-LABEL: test_vqtbx1_p8 |
| return vqtbx1_p8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| poly8x8_t test_vqtbx2_p8(poly8x8_t a, poly8x16x2_t b, uint8x8_t c) { |
| // CHECK-LABEL: test_vqtbx2_p8 |
| return vqtbx2_p8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| poly8x8_t test_vqtbx3_p8(poly8x8_t a, poly8x16x3_t b, uint8x8_t c) { |
| // CHECK-LABEL: test_vqtbx3_p8 |
| return vqtbx3_p8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| poly8x8_t test_vqtbx4_p8(poly8x8_t a, poly8x16x4_t b, uint8x8_t c) { |
| // CHECK-LABEL: test_vqtbx4_p8 |
| return vqtbx4_p8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.8b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.8b |
| } |
| |
| poly8x16_t test_vqtbx1q_p8(poly8x16_t a, uint8x16_t b, uint8x16_t c) { |
| // CHECK-LABEL: test_vqtbx1q_p8 |
| return vqtbx1q_p8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| poly8x16_t test_vqtbx2q_p8(poly8x16_t a, poly8x16x2_t b, uint8x16_t c) { |
| // CHECK-LABEL: test_vqtbx2q_p8 |
| return vqtbx2q_p8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| poly8x16_t test_vqtbx3q_p8(poly8x16_t a, poly8x16x3_t b, uint8x16_t c) { |
| // CHECK-LABEL: test_vqtbx3q_p8 |
| return vqtbx3q_p8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |
| |
| poly8x16_t test_vqtbx4q_p8(poly8x16_t a, poly8x16x4_t b, uint8x16_t c) { |
| // CHECK-LABEL: test_vqtbx4q_p8 |
| return vqtbx4q_p8(a, b, c); |
| // CHECK: tbx {{v[0-9]+}}.16b, {{{ ?v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b, v[0-9]+.16b ?}}}, {{v[0-9]+}}.16b |
| } |