From d3b97d05663da85c56dc2386ba4285e25ebc63f1 Mon Sep 17 00:00:00 2001
From: Adam <adam.niederer@gmail.com>
Date: Tue, 26 Sep 2017 22:48:20 -0400
Subject: [PATCH] Add vaddsubps

---
 library/stdarch/src/x86/avx.rs | 22 +++++++++++++++++++++-
 1 file changed, 21 insertions(+), 1 deletion(-)

diff --git a/library/stdarch/src/x86/avx.rs b/library/stdarch/src/x86/avx.rs
index b0748a55abe1..d10897dbf1eb 100644
--- a/library/stdarch/src/x86/avx.rs
+++ b/library/stdarch/src/x86/avx.rs
@@ -26,6 +26,15 @@ pub fn _mm256_addsub_pd(a: f64x4, b: f64x4) -> f64x4 {
     unsafe { addsubpd256(a, b) }
 }
 
+/// Alternatively add and subtract packed single-precision (32-bit)
+/// floating-point elements in `a` to/from packed elements in `b`.
+#[inline(always)]
+#[target_feature = "+avx"]
+#[cfg_attr(test, assert_instr(vaddsubps))]
+pub fn _mm256_addsub_ps(a: f32x8, b: f32x8) -> f32x8 {
+    unsafe { addsubps256(a, b) }
+}
+
 /// Subtract packed double-precision (64-bit) floating-point elements in `b`
 /// from packed elements in `a`.
 #[inline(always)]
@@ -90,6 +99,8 @@ pub fn _mm256_floor_pd(a: f64x4) -> f64x4 {
 extern "C" {
     #[link_name = "llvm.x86.avx.addsub.pd.256"]
     fn addsubpd256(a: f64x4, b: f64x4) -> f64x4;
+    #[link_name = "llvm.x86.avx.addsub.ps.256"]
+    fn addsubps256(a: f32x8, b: f32x8) -> f32x8;
     #[link_name = "llvm.x86.avx.round.pd.256"]
     fn roundpd256(a: f64x4, b: i32) -> f64x4;
 }
@@ -124,7 +135,16 @@ mod tests {
         let a = f64x4::new(1.0, 2.0, 3.0, 4.0);
         let b = f64x4::new(5.0, 6.0, 7.0, 8.0);
         let r = avx::_mm256_addsub_pd(a, b);
-        let e = f64x4::new(-4.0,8.0,-4.0,12.0);
+        let e = f64x4::new(-4.0, 8.0, -4.0, 12.0);
+        assert_eq!(r, e);
+    }
+
+    #[simd_test = "avx"]
+    fn _mm256_addsub_ps() {
+        let a = f32x8::new(1.0, 2.0, 3.0, 4.0, 1.0, 2.0, 3.0, 4.0);
+        let b = f32x8::new(5.0, 6.0, 7.0, 8.0, 5.0, 6.0, 7.0, 8.0);
+        let r = avx::_mm256_addsub_ps(a, b);
+        let e = f32x8::new(-4.0, 8.0, -4.0, 12.0, -4.0, 8.0, -4.0, 12.0);
         assert_eq!(r, e);
     }