在AVX中跨通道置换可以使用道内置换,然后使用_mm256_permute2f128_ps
交换通道,最后进行混合。例如,假设您要将数组{1,2,3,4,5,6,7,8}更改为{0,0,1,2,3,4,5,6},可以这样做:
__m256 t0 = _mm256_permute_ps(x, _MM_SHUFFLE(1, 0, 3, 2))
__m256 t1 = _mm256_permute2f128_ps(t0, t0, 41)
__m256 y = _mm256_blend_ps(t0, t1, 0x33)
_mm256_permute2f128_ps
也具有零化功能,这可能非常有用(另请参见Intel Intrinsics Guide Online)。我在上面的代码中使用它来交换第一条车道和第二条车道,然后将第一条车道清零。更多详情,请参见shifting-sse-avx-registers-32-bits-left-and-right-while-shifting-in-zeros。
编辑:permutevar内置函数允许运行时排列,因此不限于编译时常量。下面的代码是Agner Fog's Vector Class Library中的lookup8
函数。
static inline Vec8f lookup8(Vec8i const & index, Vec8f const & table) {
#if INSTRSET >= 8 && VECTORI256_H > 1
#if defined (_MSC_VER) && _MSC_VER < 1700 && ! defined(__INTEL_COMPILER)
return _mm256_permutevar8x32_ps(_mm256_castsi256_ps(index), _mm256_castps_si256(table));
#elif defined (GCC_VERSION) && GCC_VERSION <= 40700 && !defined(__INTEL_COMPILER) && !defined(__clang__)
return _mm256_permutevar8x32_ps(_mm256_castsi256_ps(index), table);
#else
return _mm256_permutevar8x32_ps(table, index);
#endif
#else
__m256 t1 = _mm256_castps128_ps256(_mm256_extractf128_ps(table, 1));
__m256 t2 = _mm256_insertf128_ps(t1, _mm256_castps256_ps128(table), 1);
__m256i index2 = _mm256_insertf128_si256(_mm256_castsi128_si256(index.get_low()), index.get_high(), 1);
__m256 r0 = _mm256_permutevar_ps(table, index2);
__m256 r1 = _mm256_permutevar_ps(t2, index2);
__m128i k1 = _mm_slli_epi32(index.get_high() ^ 4, 29);
__m128i k0 = _mm_slli_epi32(index.get_low(), 29);
__m256 kk = _mm256_insertf128_ps(_mm256_castps128_ps256(_mm_castsi128_ps(k0)), _mm_castsi128_ps(k1), 1);
return _mm256_blendv_ps(r0, r1, kk);
#endif
}
以下是get_low
和get_high
函数:
Vec2db get_low() const {
return _mm256_castpd256_pd128(ymm);
}
Vec2db get_high() const {
return _mm256_extractf128_pd(ymm,1);
}