OpenE2K/rust
2
0
Fork 0
Code Issues Pull Requests Projects Releases Wiki Activity

Auto merge of #32231 - ruud-v-a:avx-cmp-blend, r=alexcrichton

Browse Source 
Define AVX compare and blend intrinsics

This defines the following intrinsics:

 * `_mm256_blendv_pd`
 * `_mm256_blendv_ps`
 * `_mm256_cmp_pd`
 * `_mm256_cmp_ps`

I verified these locally.
This commit is contained in:
bors 2016-03-14 00:30:53 -07:00
commit 170f4708bb
2 changed files with 34 additions and 0 deletions
Show Stats Download Patch File Download Diff File Expand all files Collapse all files

14
src/etc/platform-intrinsics/x86/avx.json
View File

@ -8,6 +8,13 @@
"ret": "f(32-64)", "ret": "f(32-64)",
"args": ["0", "0"] "args": ["0", "0"]
}, },
{
"intrinsic": "256_blendv_{0.data_type}",
"width": [256],
"llvm": "blendv.{0.data_type}.256",
"ret": "f(32-64)",
"args": ["0", "0", "0"]
},
{ {
"intrinsic": "256_broadcast_{0.data_type}", "intrinsic": "256_broadcast_{0.data_type}",
"width": [256], "width": [256],
@ -15,6 +22,13 @@
"ret": "f(32-64)", "ret": "f(32-64)",
"args": ["s8SPc"] "args": ["s8SPc"]
}, },
{
"intrinsic": "256_cmp_{0.data_type}",
"width": [256],
"llvm": "cmp.{1.data_type}.256",
"ret": "f(32-64)",
"args": ["0", "0", "s8S"]
},
{ {
"intrinsic": "256_cvtepi32_pd", "intrinsic": "256_cvtepi32_pd",
"width": [256], "width": [256],

20
src/librustc_platform_intrinsics/x86.rs
View File

@ -498,6 +498,16 @@ pub fn find<'tcx>(_tcx: &TyCtxt<'tcx>, name: &str) -> Option<Intrinsic> {
output: v(f(64), 4), output: v(f(64), 4),
definition: Named("llvm.x86.avx.addsub.pd.256") definition: Named("llvm.x86.avx.addsub.pd.256")
}, },
"256_blendv_ps" => Intrinsic {
inputs: vec![v(f(32), 8), v(f(32), 8), v(f(32), 8)],
output: v(f(32), 8),
definition: Named("llvm.x86.avx.blendv.ps.256")
},
"256_blendv_pd" => Intrinsic {
inputs: vec![v(f(64), 4), v(f(64), 4), v(f(64), 4)],
output: v(f(64), 4),
definition: Named("llvm.x86.avx.blendv.pd.256")
},
"256_broadcast_ps" => Intrinsic { "256_broadcast_ps" => Intrinsic {
inputs: vec![p(true, i(8), None)], inputs: vec![p(true, i(8), None)],
output: v(f(32), 8), output: v(f(32), 8),
@ -508,6 +518,16 @@ pub fn find<'tcx>(_tcx: &TyCtxt<'tcx>, name: &str) -> Option<Intrinsic> {
output: v(f(64), 4), output: v(f(64), 4),
definition: Named("llvm.x86.avx.vbroadcastf128.pd.256") definition: Named("llvm.x86.avx.vbroadcastf128.pd.256")
}, },
"256_cmp_ps" => Intrinsic {
inputs: vec![v(f(32), 8), v(f(32), 8), i(8)],
output: v(f(32), 8),
definition: Named("llvm.x86.avx.cmp.ps.256")
},
"256_cmp_pd" => Intrinsic {
inputs: vec![v(f(64), 4), v(f(64), 4), i(8)],
output: v(f(64), 4),
definition: Named("llvm.x86.avx.cmp.pd.256")
},
"256_cvtepi32_pd" => Intrinsic { "256_cvtepi32_pd" => Intrinsic {
inputs: vec![v(i(32), 4)], inputs: vec![v(i(32), 4)],
output: v(f(64), 4), output: v(f(64), 4),