use core::arch::x86_64::*;
use crate::fft::{
Complex32,
butterflies::ops::{
complex_mul_avx, complex_mul_i_avx, load_neg_imag_mask_avx, load_scale_avx, v8x_avx,
w8x_avx,
},
};
#[target_feature(enable = "avx,fma")]
pub(super) unsafe fn butterfly_radix8_stride1_avx_fma(
src: &[Complex32],
dst: &mut [Complex32],
stage_twiddles: &[Complex32],
) {
let samples = src.len();
let eighth_samples = samples >> 3;
let simd_iters = (eighth_samples >> 2) << 2;
unsafe {
let neg_imag_mask = load_neg_imag_mask_avx();
let scale = load_scale_avx();
for i in (0..simd_iters).step_by(4) {
let z0_ptr = src.as_ptr().add(i) as *const f32;
let z0 = _mm256_loadu_ps(z0_ptr);
let z1_ptr = src.as_ptr().add(i + eighth_samples) as *const f32;
let z1 = _mm256_loadu_ps(z1_ptr);
let z2_ptr = src.as_ptr().add(i + eighth_samples * 2) as *const f32;
let z2 = _mm256_loadu_ps(z2_ptr);
let z3_ptr = src.as_ptr().add(i + eighth_samples * 3) as *const f32;
let z3 = _mm256_loadu_ps(z3_ptr);
let z4_ptr = src.as_ptr().add(i + eighth_samples * 4) as *const f32;
let z4 = _mm256_loadu_ps(z4_ptr);
let z5_ptr = src.as_ptr().add(i + eighth_samples * 5) as *const f32;
let z5 = _mm256_loadu_ps(z5_ptr);
let z6_ptr = src.as_ptr().add(i + eighth_samples * 6) as *const f32;
let z6 = _mm256_loadu_ps(z6_ptr);
let z7_ptr = src.as_ptr().add(i + eighth_samples * 7) as *const f32;
let z7 = _mm256_loadu_ps(z7_ptr);
let t1 = z1;
let t2 = z2;
let t3 = z3;
let t4 = z4;
let t5 = z5;
let t6 = z6;
let t7 = z7;
let even_a0 = _mm256_add_ps(z0, t4);
let even_a1 = _mm256_sub_ps(z0, t4);
let even_a2 = _mm256_add_ps(t2, t6);
let t2_sub_t6 = _mm256_sub_ps(t2, t6);
let even_a3 = complex_mul_i_avx(t2_sub_t6, neg_imag_mask);
let x_even_0 = _mm256_add_ps(even_a0, even_a2);
let x_even_2 = _mm256_sub_ps(even_a0, even_a2);
let x_even_1 = _mm256_add_ps(even_a1, even_a3);
let x_even_3 = _mm256_sub_ps(even_a1, even_a3);
let odd_a0 = _mm256_add_ps(t1, t5);
let odd_a1 = _mm256_sub_ps(t1, t5);
let odd_a2 = _mm256_add_ps(t3, t7);
let t3_sub_t7 = _mm256_sub_ps(t3, t7);
let odd_a3 = complex_mul_i_avx(t3_sub_t7, neg_imag_mask);
let x_odd_0 = _mm256_add_ps(odd_a0, odd_a2);
let x_odd_2 = _mm256_sub_ps(odd_a0, odd_a2);
let x_odd_1 = _mm256_add_ps(odd_a1, odd_a3);
let x_odd_3 = _mm256_sub_ps(odd_a1, odd_a3);
let out0 = _mm256_add_ps(x_even_0, x_odd_0);
let out4 = _mm256_sub_ps(x_even_0, x_odd_0);
let w8_1_x_odd_1 = w8x_avx(x_odd_1, neg_imag_mask, scale);
let out1 = _mm256_add_ps(x_even_1, w8_1_x_odd_1);
let out5 = _mm256_sub_ps(x_even_1, w8_1_x_odd_1);
let w8_2_x_odd_2 = complex_mul_i_avx(x_odd_2, neg_imag_mask);
let out2 = _mm256_add_ps(x_even_2, w8_2_x_odd_2);
let out6 = _mm256_sub_ps(x_even_2, w8_2_x_odd_2);
let w8_3_x_odd_3 = v8x_avx(x_odd_3, neg_imag_mask, scale);
let out3 = _mm256_add_ps(x_even_3, w8_3_x_odd_3);
let out7 = _mm256_sub_ps(x_even_3, w8_3_x_odd_3);
let j = 8 * i;
let dst_ptr = dst.as_mut_ptr().add(j) as *mut f32;
let out0_pd = _mm256_castps_pd(out0);
let out1_pd = _mm256_castps_pd(out1);
let out2_pd = _mm256_castps_pd(out2);
let out3_pd = _mm256_castps_pd(out3);
let temp_01_lo = _mm256_unpacklo_pd(out0_pd, out1_pd);
let temp_01_hi = _mm256_unpackhi_pd(out0_pd, out1_pd);
let temp_23_lo = _mm256_unpacklo_pd(out2_pd, out3_pd);
let temp_23_hi = _mm256_unpackhi_pd(out2_pd, out3_pd);
let result0 = _mm256_castpd_ps(_mm256_permute2f128_pd(temp_01_lo, temp_23_lo, 0x20));
let result2 = _mm256_castpd_ps(_mm256_permute2f128_pd(temp_01_hi, temp_23_hi, 0x20));
let result4 = _mm256_castpd_ps(_mm256_permute2f128_pd(temp_01_lo, temp_23_lo, 0x31));
let result6 = _mm256_castpd_ps(_mm256_permute2f128_pd(temp_01_hi, temp_23_hi, 0x31));
_mm256_storeu_ps(dst_ptr, result0);
_mm256_storeu_ps(dst_ptr.add(16), result2);
_mm256_storeu_ps(dst_ptr.add(32), result4);
_mm256_storeu_ps(dst_ptr.add(48), result6);
let out4_pd = _mm256_castps_pd(out4);
let out5_pd = _mm256_castps_pd(out5);
let out6_pd = _mm256_castps_pd(out6);
let out7_pd = _mm256_castps_pd(out7);
let temp_45_lo = _mm256_unpacklo_pd(out4_pd, out5_pd);
let temp_45_hi = _mm256_unpackhi_pd(out4_pd, out5_pd);
let temp_67_lo = _mm256_unpacklo_pd(out6_pd, out7_pd);
let temp_67_hi = _mm256_unpackhi_pd(out6_pd, out7_pd);
let result1 = _mm256_castpd_ps(_mm256_permute2f128_pd(temp_45_lo, temp_67_lo, 0x20));
let result3 = _mm256_castpd_ps(_mm256_permute2f128_pd(temp_45_hi, temp_67_hi, 0x20));
let result5 = _mm256_castpd_ps(_mm256_permute2f128_pd(temp_45_lo, temp_67_lo, 0x31));
let result7 = _mm256_castpd_ps(_mm256_permute2f128_pd(temp_45_hi, temp_67_hi, 0x31));
_mm256_storeu_ps(dst_ptr.add(8), result1);
_mm256_storeu_ps(dst_ptr.add(24), result3);
_mm256_storeu_ps(dst_ptr.add(40), result5);
_mm256_storeu_ps(dst_ptr.add(56), result7);
}
}
super::butterfly_radix8_scalar::<4>(src, dst, stage_twiddles, 1, simd_iters);
}
#[target_feature(enable = "avx,fma")]
pub(super) unsafe fn butterfly_radix8_generic_avx_fma(
src: &[Complex32],
dst: &mut [Complex32],
stage_twiddles: &[Complex32],
stride: usize,
) {
if stride == 0 {
return;
}
let samples = src.len();
let eighth_samples = samples >> 3;
let simd_iters = (eighth_samples >> 2) << 2;
unsafe {
let neg_imag_mask = load_neg_imag_mask_avx();
let scale = load_scale_avx();
for i in (0..simd_iters).step_by(4) {
let k = i % stride;
let k0 = k;
let k1 = k + 1 - ((k + 1 >= stride) as usize) * stride;
let k2 = k + 2 - ((k + 2 >= stride) as usize) * stride;
let k3 = k + 3 - ((k + 3 >= stride) as usize) * stride;
let z0_ptr = src.as_ptr().add(i) as *const f32;
let z0 = _mm256_loadu_ps(z0_ptr);
let z1_ptr = src.as_ptr().add(i + eighth_samples) as *const f32;
let z1 = _mm256_loadu_ps(z1_ptr);
let z2_ptr = src.as_ptr().add(i + eighth_samples * 2) as *const f32;
let z2 = _mm256_loadu_ps(z2_ptr);
let z3_ptr = src.as_ptr().add(i + eighth_samples * 3) as *const f32;
let z3 = _mm256_loadu_ps(z3_ptr);
let z4_ptr = src.as_ptr().add(i + eighth_samples * 4) as *const f32;
let z4 = _mm256_loadu_ps(z4_ptr);
let z5_ptr = src.as_ptr().add(i + eighth_samples * 5) as *const f32;
let z5 = _mm256_loadu_ps(z5_ptr);
let z6_ptr = src.as_ptr().add(i + eighth_samples * 6) as *const f32;
let z6 = _mm256_loadu_ps(z6_ptr);
let z7_ptr = src.as_ptr().add(i + eighth_samples * 7) as *const f32;
let z7 = _mm256_loadu_ps(z7_ptr);
let tw_ptr = stage_twiddles.as_ptr().add(i * 7) as *const f32;
let w1 = _mm256_loadu_ps(tw_ptr); let w2 = _mm256_loadu_ps(tw_ptr.add(8)); let w3 = _mm256_loadu_ps(tw_ptr.add(16)); let w4 = _mm256_loadu_ps(tw_ptr.add(24)); let w5 = _mm256_loadu_ps(tw_ptr.add(32)); let w6 = _mm256_loadu_ps(tw_ptr.add(40)); let w7 = _mm256_loadu_ps(tw_ptr.add(48));
let t1 = complex_mul_avx(w1, z1);
let t2 = complex_mul_avx(w2, z2);
let t3 = complex_mul_avx(w3, z3);
let t4 = complex_mul_avx(w4, z4);
let t5 = complex_mul_avx(w5, z5);
let t6 = complex_mul_avx(w6, z6);
let t7 = complex_mul_avx(w7, z7);
let even_a0 = _mm256_add_ps(z0, t4);
let even_a1 = _mm256_sub_ps(z0, t4);
let even_a2 = _mm256_add_ps(t2, t6);
let t2_sub_t6 = _mm256_sub_ps(t2, t6);
let even_a3 = complex_mul_i_avx(t2_sub_t6, neg_imag_mask);
let x_even_0 = _mm256_add_ps(even_a0, even_a2);
let x_even_2 = _mm256_sub_ps(even_a0, even_a2);
let x_even_1 = _mm256_add_ps(even_a1, even_a3);
let x_even_3 = _mm256_sub_ps(even_a1, even_a3);
let odd_a0 = _mm256_add_ps(t1, t5);
let odd_a1 = _mm256_sub_ps(t1, t5);
let odd_a2 = _mm256_add_ps(t3, t7);
let t3_sub_t7 = _mm256_sub_ps(t3, t7);
let odd_a3 = complex_mul_i_avx(t3_sub_t7, neg_imag_mask);
let x_odd_0 = _mm256_add_ps(odd_a0, odd_a2);
let x_odd_2 = _mm256_sub_ps(odd_a0, odd_a2);
let x_odd_1 = _mm256_add_ps(odd_a1, odd_a3);
let x_odd_3 = _mm256_sub_ps(odd_a1, odd_a3);
let out0 = _mm256_add_ps(x_even_0, x_odd_0);
let out4 = _mm256_sub_ps(x_even_0, x_odd_0);
let w8_1_x_odd_1 = w8x_avx(x_odd_1, neg_imag_mask, scale);
let out1 = _mm256_add_ps(x_even_1, w8_1_x_odd_1);
let out5 = _mm256_sub_ps(x_even_1, w8_1_x_odd_1);
let w8_2_x_odd_2 = complex_mul_i_avx(x_odd_2, neg_imag_mask);
let out2 = _mm256_add_ps(x_even_2, w8_2_x_odd_2);
let out6 = _mm256_sub_ps(x_even_2, w8_2_x_odd_2);
let w8_3_x_odd_3 = v8x_avx(x_odd_3, neg_imag_mask, scale);
let out3 = _mm256_add_ps(x_even_3, w8_3_x_odd_3);
let out7 = _mm256_sub_ps(x_even_3, w8_3_x_odd_3);
let j0 = 8 * i - 7 * k0;
let j1 = 8 * (i + 1) - 7 * k1;
let j2 = 8 * (i + 2) - 7 * k2;
let j3 = 8 * (i + 3) - 7 * k3;
let dst_ptr = dst.as_mut_ptr() as *mut f64;
let out0_pd = _mm256_castps_pd(out0);
let out1_pd = _mm256_castps_pd(out1);
let out2_pd = _mm256_castps_pd(out2);
let out3_pd = _mm256_castps_pd(out3);
let out0_lo = _mm256_castpd256_pd128(out0_pd);
let out0_hi = _mm256_extractf128_pd(out0_pd, 1);
let out1_lo = _mm256_castpd256_pd128(out1_pd);
let out1_hi = _mm256_extractf128_pd(out1_pd, 1);
let out2_lo = _mm256_castpd256_pd128(out2_pd);
let out2_hi = _mm256_extractf128_pd(out2_pd, 1);
let out3_lo = _mm256_castpd256_pd128(out3_pd);
let out3_hi = _mm256_extractf128_pd(out3_pd, 1);
_mm_storel_pd(dst_ptr.add(j0), out0_lo);
_mm_storel_pd(dst_ptr.add(j0 + stride), out1_lo);
_mm_storel_pd(dst_ptr.add(j0 + stride * 2), out2_lo);
_mm_storel_pd(dst_ptr.add(j0 + stride * 3), out3_lo);
_mm_storeh_pd(dst_ptr.add(j1), out0_lo);
_mm_storeh_pd(dst_ptr.add(j1 + stride), out1_lo);
_mm_storeh_pd(dst_ptr.add(j1 + stride * 2), out2_lo);
_mm_storeh_pd(dst_ptr.add(j1 + stride * 3), out3_lo);
_mm_storel_pd(dst_ptr.add(j2), out0_hi);
_mm_storel_pd(dst_ptr.add(j2 + stride), out1_hi);
_mm_storel_pd(dst_ptr.add(j2 + stride * 2), out2_hi);
_mm_storel_pd(dst_ptr.add(j2 + stride * 3), out3_hi);
_mm_storeh_pd(dst_ptr.add(j3), out0_hi);
_mm_storeh_pd(dst_ptr.add(j3 + stride), out1_hi);
_mm_storeh_pd(dst_ptr.add(j3 + stride * 2), out2_hi);
_mm_storeh_pd(dst_ptr.add(j3 + stride * 3), out3_hi);
let out4_pd = _mm256_castps_pd(out4);
let out5_pd = _mm256_castps_pd(out5);
let out6_pd = _mm256_castps_pd(out6);
let out7_pd = _mm256_castps_pd(out7);
let out4_lo = _mm256_castpd256_pd128(out4_pd);
let out4_hi = _mm256_extractf128_pd(out4_pd, 1);
let out5_lo = _mm256_castpd256_pd128(out5_pd);
let out5_hi = _mm256_extractf128_pd(out5_pd, 1);
let out6_lo = _mm256_castpd256_pd128(out6_pd);
let out6_hi = _mm256_extractf128_pd(out6_pd, 1);
let out7_lo = _mm256_castpd256_pd128(out7_pd);
let out7_hi = _mm256_extractf128_pd(out7_pd, 1);
_mm_storel_pd(dst_ptr.add(j0 + stride * 4), out4_lo);
_mm_storel_pd(dst_ptr.add(j0 + stride * 5), out5_lo);
_mm_storel_pd(dst_ptr.add(j0 + stride * 6), out6_lo);
_mm_storel_pd(dst_ptr.add(j0 + stride * 7), out7_lo);
_mm_storeh_pd(dst_ptr.add(j1 + stride * 4), out4_lo);
_mm_storeh_pd(dst_ptr.add(j1 + stride * 5), out5_lo);
_mm_storeh_pd(dst_ptr.add(j1 + stride * 6), out6_lo);
_mm_storeh_pd(dst_ptr.add(j1 + stride * 7), out7_lo);
_mm_storel_pd(dst_ptr.add(j2 + stride * 4), out4_hi);
_mm_storel_pd(dst_ptr.add(j2 + stride * 5), out5_hi);
_mm_storel_pd(dst_ptr.add(j2 + stride * 6), out6_hi);
_mm_storel_pd(dst_ptr.add(j2 + stride * 7), out7_hi);
_mm_storeh_pd(dst_ptr.add(j3 + stride * 4), out4_hi);
_mm_storeh_pd(dst_ptr.add(j3 + stride * 5), out5_hi);
_mm_storeh_pd(dst_ptr.add(j3 + stride * 6), out6_hi);
_mm_storeh_pd(dst_ptr.add(j3 + stride * 7), out7_hi);
}
}
super::butterfly_radix8_scalar::<4>(src, dst, stage_twiddles, stride, simd_iters);
}