[Date Prev][Date Next][Thread Prev][Thread Next][Date Index][Thread Index]
[Qemu-devel] [PATCH 02/10] cutils: Remove SPLAT macro
From: |
Paolo Bonzini |
Subject: |
[Qemu-devel] [PATCH 02/10] cutils: Remove SPLAT macro |
Date: |
Tue, 13 Sep 2016 18:09:57 +0200 |
From: Richard Henderson <address@hidden>
This is unused and complicates the vector interface.
Signed-off-by: Richard Henderson <address@hidden>
Message-Id: <address@hidden>
Signed-off-by: Paolo Bonzini <address@hidden>
---
util/bufferiszero.c | 4 ----
1 file changed, 4 deletions(-)
diff --git a/util/bufferiszero.c b/util/bufferiszero.c
index 9bb1ae5..067d08f 100644
--- a/util/bufferiszero.c
+++ b/util/bufferiszero.c
@@ -37,7 +37,6 @@
#undef pixel
#undef bool
#define VECTYPE __vector unsigned char
-#define SPLAT(p) vec_splat(vec_ld(0, p), 0)
#define ALL_EQ(v1, v2) vec_all_eq(v1, v2)
#define VEC_OR(v1, v2) ((v1) | (v2))
/* altivec.h may redefine the bool macro as vector type.
@@ -46,7 +45,6 @@
#elif defined __SSE2__
#include <emmintrin.h>
#define VECTYPE __m128i
-#define SPLAT(p) _mm_set1_epi8(*(p))
#define ALL_EQ(v1, v2) (_mm_movemask_epi8(_mm_cmpeq_epi8(v1, v2)) == 0xFFFF)
#define VEC_OR(v1, v2) (_mm_or_si128(v1, v2))
#elif defined(__aarch64__)
@@ -58,7 +56,6 @@
#define VEC_OR(v1, v2) ((v1) | (v2))
#else
#define VECTYPE unsigned long
-#define SPLAT(p) (*(p) * (~0UL / 255))
#define ALL_EQ(v1, v2) ((v1) == (v2))
#define VEC_OR(v1, v2) ((v1) | (v2))
#endif
@@ -135,7 +132,6 @@ static size_t buffer_find_nonzero_offset_inner(const void
*buf, size_t len)
#include <immintrin.h>
#define AVX2_VECTYPE __m256i
-#define AVX2_SPLAT(p) _mm256_set1_epi8(*(p))
#define AVX2_ALL_EQ(v1, v2) \
(_mm256_movemask_epi8(_mm256_cmpeq_epi8(v1, v2)) == 0xFFFFFFFF)
#define AVX2_VEC_OR(v1, v2) (_mm256_or_si256(v1, v2))
--
1.8.3.1
- [Qemu-devel] [PATCH v4 00/10] Improve buffer_is_zero, Paolo Bonzini, 2016/09/13
- [Qemu-devel] [PATCH 01/10] cutils: Move buffer_is_zero and subroutines to a new file, Paolo Bonzini, 2016/09/13
- [Qemu-devel] [PATCH 04/10] cutils: Rearrange buffer_is_zero acceleration, Paolo Bonzini, 2016/09/13
- [Qemu-devel] [PATCH 03/10] cutils: Export only buffer_is_zero, Paolo Bonzini, 2016/09/13
- [Qemu-devel] [PATCH 05/10] cutils: Remove aarch64 buffer zero checking, Paolo Bonzini, 2016/09/13
- [Qemu-devel] [PATCH 02/10] cutils: Remove SPLAT macro,
Paolo Bonzini <=
- [Qemu-devel] [PATCH 07/10] cutils: Add test for buffer_is_zero, Paolo Bonzini, 2016/09/13
- [Qemu-devel] [PATCH 06/10] cutils: Remove ppc buffer zero checking, Paolo Bonzini, 2016/09/13
- [Qemu-devel] [PATCH 08/10] cutils: Add SSE4 version, Paolo Bonzini, 2016/09/13
- [Qemu-devel] [PATCH 09/10] cutils: Add generic prefetch, Paolo Bonzini, 2016/09/13
- [Qemu-devel] [PATCH 10/10] cutils: Rewrite x86 buffer zero checking, Paolo Bonzini, 2016/09/13