diff options
author | RĂ©mi Verschelde <remi@verschelde.fr> | 2021-05-21 18:30:02 +0200 |
---|---|---|
committer | GitHub <noreply@github.com> | 2021-05-21 18:30:02 +0200 |
commit | 3ee034451a9349e7de26decc662afefd7ab8c460 (patch) | |
tree | a8bec3fbb06c2eaca05a075f5ffe2cdd2d94f04a /thirdparty/embree-aarch64/common/simd/vboold8_avx512.h | |
parent | 8fa07eae145e1e37eb8708ce8c117188b58e3ecc (diff) | |
parent | 767e374dced69b45db0afb30ca2ccf0bbbeef672 (diff) |
Merge pull request #48885 from JFonS/upgrade_embree
Upgrade Embree to the latest official release (3.13.0).
Diffstat (limited to 'thirdparty/embree-aarch64/common/simd/vboold8_avx512.h')
-rw-r--r-- | thirdparty/embree-aarch64/common/simd/vboold8_avx512.h | 148 |
1 files changed, 0 insertions, 148 deletions
diff --git a/thirdparty/embree-aarch64/common/simd/vboold8_avx512.h b/thirdparty/embree-aarch64/common/simd/vboold8_avx512.h deleted file mode 100644 index fdf3f00de5..0000000000 --- a/thirdparty/embree-aarch64/common/simd/vboold8_avx512.h +++ /dev/null @@ -1,148 +0,0 @@ -// Copyright 2009-2020 Intel Corporation -// SPDX-License-Identifier: Apache-2.0 - -#pragma once - -namespace embree -{ - /* 8-wide AVX-512 bool type */ - template<> - struct vboold<8> - { - typedef vboold8 Bool; - typedef vint8 Int; - - enum { size = 8 }; // number of SIMD elements - __mmask8 v; // data - - //////////////////////////////////////////////////////////////////////////////// - /// Constructors, Assignment & Cast Operators - //////////////////////////////////////////////////////////////////////////////// - - __forceinline vboold() {} - __forceinline vboold(const vboold8& t) { v = t.v; } - __forceinline vboold8& operator =(const vboold8& f) { v = f.v; return *this; } - - __forceinline vboold(const __mmask8& t) { v = t; } - __forceinline operator __mmask8() const { return v; } - - __forceinline vboold(bool b) { v = b ? 0xff : 0x00; } - __forceinline vboold(int t) { v = (__mmask8)t; } - __forceinline vboold(unsigned int t) { v = (__mmask8)t; } - - /* return int8 mask */ - __forceinline __m128i mask8() const { -#if defined(__AVX512BW__) - return _mm_movm_epi8(v); -#else - const __m512i f = _mm512_set1_epi64(0); - const __m512i t = _mm512_set1_epi64(-1); - const __m512i m = _mm512_mask_or_epi64(f,v,t,t); - return _mm512_cvtepi64_epi8(m); -#endif - } - - /* return int64 mask */ - __forceinline __m512i mask64() const { -#if defined(__AVX512DQ__) - return _mm512_movm_epi64(v); -#else - const __m512i f = _mm512_set1_epi64(0); - const __m512i t = _mm512_set1_epi64(-1); - return _mm512_mask_or_epi64(f,v,t,t); -#endif - } - - //////////////////////////////////////////////////////////////////////////////// - /// Constants - //////////////////////////////////////////////////////////////////////////////// - - __forceinline vboold(FalseTy) : v(0x00) {} - __forceinline vboold(TrueTy) : v(0xff) {} - - //////////////////////////////////////////////////////////////////////////////// - /// Array Access - //////////////////////////////////////////////////////////////////////////////// - - __forceinline bool operator [](size_t index) const { - assert(index < 8); return (mm512_mask2int(v) >> index) & 1; - } - }; - - //////////////////////////////////////////////////////////////////////////////// - /// Unary Operators - //////////////////////////////////////////////////////////////////////////////// - - __forceinline vboold8 operator !(const vboold8& a) { return _mm512_knot(a); } - - //////////////////////////////////////////////////////////////////////////////// - /// Binary Operators - //////////////////////////////////////////////////////////////////////////////// - - __forceinline vboold8 operator &(const vboold8& a, const vboold8& b) { return _mm512_kand(a, b); } - __forceinline vboold8 operator |(const vboold8& a, const vboold8& b) { return _mm512_kor(a, b); } - __forceinline vboold8 operator ^(const vboold8& a, const vboold8& b) { return _mm512_kxor(a, b); } - - __forceinline vboold8 andn(const vboold8& a, const vboold8& b) { return _mm512_kandn(b, a); } - - //////////////////////////////////////////////////////////////////////////////// - /// Assignment Operators - //////////////////////////////////////////////////////////////////////////////// - - __forceinline vboold8& operator &=(vboold8& a, const vboold8& b) { return a = a & b; } - __forceinline vboold8& operator |=(vboold8& a, const vboold8& b) { return a = a | b; } - __forceinline vboold8& operator ^=(vboold8& a, const vboold8& b) { return a = a ^ b; } - - //////////////////////////////////////////////////////////////////////////////// - /// Comparison Operators + Select - //////////////////////////////////////////////////////////////////////////////// - - __forceinline vboold8 operator !=(const vboold8& a, const vboold8& b) { return _mm512_kxor(a, b); } - __forceinline vboold8 operator ==(const vboold8& a, const vboold8& b) { return _mm512_kxnor(a, b); } - - __forceinline vboold8 select(const vboold8& s, const vboold8& a, const vboold8& b) { - return _mm512_kor(_mm512_kand(s, a), _mm512_kandn(s, b)); - } - - //////////////////////////////////////////////////////////////////////////////// - /// Reduction Operations - //////////////////////////////////////////////////////////////////////////////// - - __forceinline int all (const vboold8& a) { return a.v == 0xff; } - __forceinline int any (const vboold8& a) { return _mm512_kortestz(a, a) == 0; } - __forceinline int none(const vboold8& a) { return _mm512_kortestz(a, a) != 0; } - - __forceinline int all (const vboold8& valid, const vboold8& b) { return all((!valid) | b); } - __forceinline int any (const vboold8& valid, const vboold8& b) { return any(valid & b); } - __forceinline int none(const vboold8& valid, const vboold8& b) { return none(valid & b); } - - __forceinline size_t movemask(const vboold8& a) { return _mm512_kmov(a); } - __forceinline size_t popcnt (const vboold8& a) { return popcnt(a.v); } - - //////////////////////////////////////////////////////////////////////////////// - /// Conversion Operations - //////////////////////////////////////////////////////////////////////////////// - - __forceinline unsigned int toInt(const vboold8& a) { return mm512_mask2int(a); } - - //////////////////////////////////////////////////////////////////////////////// - /// Get/Set Functions - //////////////////////////////////////////////////////////////////////////////// - - __forceinline bool get(const vboold8& a, size_t index) { assert(index < 8); return (toInt(a) >> index) & 1; } - __forceinline void set(vboold8& a, size_t index) { assert(index < 8); a |= 1 << index; } - __forceinline void clear(vboold8& a, size_t index) { assert(index < 8); a = andn(a, 1 << index); } - - //////////////////////////////////////////////////////////////////////////////// - /// Output Operators - //////////////////////////////////////////////////////////////////////////////// - - __forceinline embree_ostream operator <<(embree_ostream cout, const vboold8& a) - { - cout << "<"; - for (size_t i=0; i<8; i++) { - if ((a.v >> i) & 1) cout << "1"; else cout << "0"; - } - return cout << ">"; - } -} |