mirrors/pipewire
1
0
Fork 0
mirror of https://gitlab.freedesktop.org/pipewire/pipewire.git synced 2025-11-02 09:01:50 -05:00
Code Issues Projects Releases Packages Wiki Activity Actions

plugin: workaround for AVX intrinsic: "_mm256_setr_m128()" missing in GCC

Browse source 
Signed-off-by: Martin Koch <martin.koch@ese.de>
This commit is contained in:
Martin Koch 2020-05-13 10:23:05 +02:00 • committed by Wim Taymans
parent cee1a26be6
commit fefdc26f84
1 changed files with 10 additions and 2 deletions
Download patch file Download diff file Expand all files Collapse all files

12
spa/plugins/audioconvert/fmt-ops-avx2.c
View file

@ -25,6 +25,14 @@
#include "fmt-ops.h" #include "fmt-ops.h"
#include <immintrin.h> #include <immintrin.h>
// GCC: workaround for missing AVX intrinsic: "_mm256_setr_m128()"
// (see https://stackoverflow.com/questions/32630458/setting-m256i-to-the-value-of-two-m128i-values)
#ifndef _mm256_setr_m128i
# ifndef _mm256_set_m128i
# define _mm256_set_m128i(v0, v1) _mm256_insertf128_si256(_mm256_castsi128_si256(v1), (v0), 1)
# endif
# define _mm256_setr_m128i(v0, v1) _mm256_set_m128i((v1), (v0))
#endif
static void static void
conv_s16_to_f32d_1s_avx2(void *data, void * SPA_RESTRICT dst[], const void * SPA_RESTRICT src, conv_s16_to_f32d_1s_avx2(void *data, void * SPA_RESTRICT dst[], const void * SPA_RESTRICT src,
@ -489,10 +497,10 @@ conv_s32_to_f32d_1s_avx2(void *data, void * SPA_RESTRICT dst[], const void * SPA
for(n = 0; n < unrolled; n += 16) { for(n = 0; n < unrolled; n += 16) {
in[0] = _mm256_setr_m128i( in[0] = _mm256_setr_m128i(
_mm256_i64gather_epi32(&s[ 0*n_channels], mask1, 4), _mm256_i64gather_epi32(&s[ 0*n_channels], mask1, 4),
_mm256_i64gather_epi32(&s[ 0*n_channels], mask2, 4)), _mm256_i64gather_epi32(&s[ 0*n_channels], mask2, 4));
in[1] = _mm256_setr_m128i( in[1] = _mm256_setr_m128i(
_mm256_i64gather_epi32(&s[ 8*n_channels], mask1, 4), _mm256_i64gather_epi32(&s[ 8*n_channels], mask1, 4),
_mm256_i64gather_epi32(&s[ 8*n_channels], mask2, 4)), _mm256_i64gather_epi32(&s[ 8*n_channels], mask2, 4));
in[0] = _mm256_srai_epi32(in[0], 8); in[0] = _mm256_srai_epi32(in[0], 8);
in[1] = _mm256_srai_epi32(in[1], 8); in[1] = _mm256_srai_epi32(in[1], 8);