diff options
Diffstat (limited to 'gcc-4.9/gcc/testsuite/gcc.target/i386/avx2-mpsadbw-2.c')
-rw-r--r-- | gcc-4.9/gcc/testsuite/gcc.target/i386/avx2-mpsadbw-2.c | 132 |
1 files changed, 132 insertions, 0 deletions
diff --git a/gcc-4.9/gcc/testsuite/gcc.target/i386/avx2-mpsadbw-2.c b/gcc-4.9/gcc/testsuite/gcc.target/i386/avx2-mpsadbw-2.c new file mode 100644 index 000000000..18118e442 --- /dev/null +++ b/gcc-4.9/gcc/testsuite/gcc.target/i386/avx2-mpsadbw-2.c @@ -0,0 +1,132 @@ +/* { dg-do run } */ +/* { dg-require-effective-target avx2 } */ +/* { dg-options "-O2 -mavx2" } */ + +#include <string.h> +#include "avx2-check.h" + +#define msk0 0xC0 +#define msk1 0x01 +#define msk2 0xF2 +#define msk3 0x03 +#define msk4 0x84 +#define msk5 0x05 +#define msk6 0xE6 +#define msk7 0x67 + + +static void +compute_mpsadbw (int *i1, int *i2, int mask, int *r) +{ + unsigned char s[4]; + int i, j; + int offs1, offs2; + unsigned char *v1 = (char *) i1; + unsigned char *v2 = (char *) i2; + unsigned short *ret = (unsigned short *) r; + + memset (ret, 0, 32); + + /* Lower part */ + offs2 = 4 * (mask & 3); + for (i = 0; i < 4; i++) + s[i] = v2[offs2 + i]; + + offs1 = 4 * ((mask & 4) >> 2); + for (j = 0; j < 8; j++) + for (i = 0; i < 4; i++) + ret[j] += abs (v1[offs1 + j + i] - s[i]); + + /* Higher part */ + offs2 = 4 * ((mask >> 3) & 3) + 16; + for (i = 0; i < 4; i++) + s[i] = v2[offs2 + i]; + + offs1 = 4 * ((mask & 0x20) >> 5) + 16; + for (j = 0; j < 8; j++) + for (i = 0; i < 4; i++) + ret[j + 8] += abs (v1[offs1 + j + i] - s[i]); +} + +static void +avx2_test (void) +{ + union256i_d val1, val2, val3[8], res[8]; + int tmp[8]; + unsigned char masks[8]; + int i, j; + + val1.a[0] = 0x35251505; + val1.a[1] = 0x75655545; + val1.a[2] = 0xB5A59585; + val1.a[3] = 0xF5E5D5C5; + + val1.a[4] = 0x35251505; + val1.a[5] = 0x75655545; + val1.a[6] = 0xB5A59585; + val1.a[7] = 0xF5E5D5C5; + + val2.a[0] = 0x31211101; + val2.a[1] = 0x71615141; + val2.a[2] = 0xB1A19181; + val2.a[3] = 0xF1E1D1C1; + + val2.a[4] = 0x31211101; + val2.a[5] = 0x71615141; + val2.a[6] = 0xB1A19181; + val2.a[7] = 0xF1E1D1C1; + + for (i = 0; i < 8; i++) + switch (i % 3) + { + case 1: + val3[i].a[0] = 0xF1E1D1C1; + val3[i].a[1] = 0xB1A19181; + val3[i].a[2] = 0x71615141; + val3[i].a[3] = 0x31211101; + break; + default: + val3[i].x = val2.x; + break; + } + + /* Check mpsadbw imm8, ymm, ymm. */ + res[0].x = _mm256_mpsadbw_epu8 (val1.x, val2.x, msk0); + res[1].x = _mm256_mpsadbw_epu8 (val1.x, val2.x, msk1); + res[2].x = _mm256_mpsadbw_epu8 (val1.x, val2.x, msk2); + res[3].x = _mm256_mpsadbw_epu8 (val1.x, val2.x, msk3); + res[4].x = _mm256_mpsadbw_epu8 (val1.x, val2.x, msk4); + res[5].x = _mm256_mpsadbw_epu8 (val1.x, val2.x, msk5); + res[6].x = _mm256_mpsadbw_epu8 (val1.x, val2.x, msk6); + res[7].x = _mm256_mpsadbw_epu8 (val1.x, val2.x, msk7); + + masks[0] = msk0; + masks[1] = msk1; + masks[2] = msk2; + masks[3] = msk3; + masks[4] = msk4; + masks[5] = msk5; + masks[6] = msk6; + masks[7] = msk7; + + for (i = 0; i < 8; i++) + { + compute_mpsadbw (val1.a, val2.a, masks[i], tmp); + if (check_union256i_d (res[i], tmp)) + abort (); + } + + /* Check mpsadbw imm8, m256, ymm. */ + for (i = 0; i < 8; i++) + { + res[i].x = _mm256_mpsadbw_epu8 (val1.x, val3[i].x, msk4); + masks[i] = msk4; + } + + for (i = 0; i < 8; i++) + { + compute_mpsadbw (val1.a, val3[i].a, masks[i], tmp); + if (check_union256i_d (res[i], tmp)) + abort (); + } +} |