| /* { dg-do run } */ |
| /* { dg-options "-mavx2 -O2" } */ |
| /* { dg-require-effective-target avx2 } */ |
| |
| #include "avx2-check.h" |
| #include "ssse3-vals.h" |
| |
| static short |
| signed_saturate_to_word (int x) |
| { |
| if (x > (int) 0x7fff) |
| return 0x7fff; |
| |
| if (x < (int) 0xffff8000) |
| return 0x8000; |
| |
| return (short) x; |
| } |
| |
| static void |
| compute_phsubsw256 (short *i1, short *i2, short *r) |
| { |
| int i; |
| |
| for (i = 0; i < 4; i++) |
| r[i + 0] = signed_saturate_to_word (i1[2 * i] - i1[2 * i + 1]); |
| |
| for (i = 0; i < 4; i++) |
| r[i + 4] = signed_saturate_to_word (i2[2 * i] - i2[2 * i + 1]); |
| |
| for (i = 0; i < 4; i++) |
| r[i + 8] = signed_saturate_to_word (i1[2 * i + 8] - i1[2 * i + 9]); |
| |
| for (i = 0; i < 4; i++) |
| r[i + 12] = signed_saturate_to_word (i2[2 * i + 8] - i2[2 * i + 9]); |
| } |
| |
| static void |
| avx2_test (void) |
| { |
| union256i_w s1, s2, res; |
| short res_ref[16]; |
| int i; |
| int fail = 0; |
| |
| for (i = 0; i < 256; i += 16) |
| { |
| s1.x = _mm256_loadu_si256 ((__m256i *) & vals[i]); |
| s2.x = _mm256_loadu_si256 ((__m256i *) & vals[i + 8]); |
| |
| res.x = _mm256_hsubs_epi16 (s1.x, s2.x); |
| |
| compute_phsubsw256 (s1.a, s2.a, res_ref); |
| |
| fail += check_union256i_w (res, res_ref); |
| } |
| |
| if (fail != 0) |
| abort (); |
| } |