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

audioconvert: fix distorted audio on AVX2

Browse source 
Closes pipewire/pipewire#2885

Signed-off-by: Sefa Eyeoglu <contact@scrumplex.net>
This commit is contained in:
Sefa Eyeoglu 2022-12-11 20:14:09 +01:00
parent 8c892443eb
commit b927063b89
No known key found for this signature in database
GPG key ID: C10411294912A422
1 changed files with 3 additions and 3 deletions
Download patch file Download diff file Expand all files Collapse all files

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

@ -339,7 +339,7 @@ conv_s32_to_f32d_4s_avx2(void *data, void * SPA_RESTRICT dst[], const void * SPA
__m256i in[4]; __m256i in[4];
__m256 out[4], factor = _mm256_set1_ps(1.0f / S24_SCALE); __m256 out[4], factor = _mm256_set1_ps(1.0f / S24_SCALE);
__m256i mask1 = _mm256_setr_epi32(0*n_channels, 1*n_channels, 2*n_channels, 3*n_channels, __m256i mask1 = _mm256_setr_epi32(0*n_channels, 1*n_channels, 2*n_channels, 3*n_channels,
3*n_channels, 5*n_channels, 6*n_channels, 7*n_channels); 4*n_channels, 5*n_channels, 6*n_channels, 7*n_channels);
if (SPA_IS_ALIGNED(d0, 32) && if (SPA_IS_ALIGNED(d0, 32) &&
SPA_IS_ALIGNED(d1, 32) && SPA_IS_ALIGNED(d1, 32) &&
@ -405,7 +405,7 @@ conv_s32_to_f32d_2s_avx2(void *data, void * SPA_RESTRICT dst[], const void * SPA
__m256i in[4]; __m256i in[4];
__m256 out[4], factor = _mm256_set1_ps(1.0f / S24_SCALE); __m256 out[4], factor = _mm256_set1_ps(1.0f / S24_SCALE);
__m256i mask1 = _mm256_setr_epi32(0*n_channels, 1*n_channels, 2*n_channels, 3*n_channels, __m256i mask1 = _mm256_setr_epi32(0*n_channels, 1*n_channels, 2*n_channels, 3*n_channels,
3*n_channels, 5*n_channels, 6*n_channels, 7*n_channels); 4*n_channels, 5*n_channels, 6*n_channels, 7*n_channels);
if (SPA_IS_ALIGNED(d0, 32) && if (SPA_IS_ALIGNED(d0, 32) &&
SPA_IS_ALIGNED(d1, 32)) SPA_IS_ALIGNED(d1, 32))
@ -453,7 +453,7 @@ conv_s32_to_f32d_1s_avx2(void *data, void * SPA_RESTRICT dst[], const void * SPA
__m256i in[2]; __m256i in[2];
__m256 out[2], factor = _mm256_set1_ps(1.0f / S24_SCALE); __m256 out[2], factor = _mm256_set1_ps(1.0f / S24_SCALE);
__m256i mask1 = _mm256_setr_epi32(0*n_channels, 1*n_channels, 2*n_channels, 3*n_channels, __m256i mask1 = _mm256_setr_epi32(0*n_channels, 1*n_channels, 2*n_channels, 3*n_channels,
3*n_channels, 5*n_channels, 6*n_channels, 7*n_channels); 4*n_channels, 5*n_channels, 6*n_channels, 7*n_channels);
if (SPA_IS_ALIGNED(d0, 32)) if (SPA_IS_ALIGNED(d0, 32))
unrolled = n_samples & ~15; unrolled = n_samples & ~15;