[Date Prev][Date Next][Thread Prev][Thread Next][Date Index][Thread Index]
[Qemu-devel] [PATCH 1/7] cutils: Remove SPLAT macro
From: |
Richard Henderson |
Subject: |
[Qemu-devel] [PATCH 1/7] cutils: Remove SPLAT macro |
Date: |
Tue, 23 Aug 2016 21:17:53 -0700 |
This is unused and complicates the vector interface.
Signed-off-by: Richard Henderson <address@hidden>
---
util/cutils.c | 4 ----
1 file changed, 4 deletions(-)
diff --git a/util/cutils.c b/util/cutils.c
index 7505fda..1c8635c 100644
--- a/util/cutils.c
+++ b/util/cutils.c
@@ -172,7 +172,6 @@ int qemu_fdatasync(int fd)
#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.
@@ -181,7 +180,6 @@ int qemu_fdatasync(int fd)
#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__)
@@ -193,7 +191,6 @@ int qemu_fdatasync(int fd)
#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
@@ -270,7 +267,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))
--
2.7.4
- [Qemu-devel] [PATCH 0/7] Improve buffer_is_zero, Richard Henderson, 2016/08/24
- [Qemu-devel] [PATCH 4/7] cutils: Add generic prefetch, Richard Henderson, 2016/08/24
- [Qemu-devel] [PATCH 2/7] cutils: Export only buffer_is_zero, Richard Henderson, 2016/08/24
- [Qemu-devel] [PATCH 1/7] cutils: Remove SPLAT macro,
Richard Henderson <=
- [Qemu-devel] [PATCH 3/7] cutils: Rearrange buffer_is_zero acceleration, Richard Henderson, 2016/08/24
- [Qemu-devel] [PATCH 5/7] cutils: Rewrite x86 buffer zero checking, Richard Henderson, 2016/08/24
- [Qemu-devel] [PATCH 6/7] cutils: Rewrite aarch64 buffer zero checking, Richard Henderson, 2016/08/24
- [Qemu-devel] [PATCH 7/7] cutils: Rewrite ppc buffer zero checking, Richard Henderson, 2016/08/24
- Re: [Qemu-devel] [PATCH 0/7] Improve buffer_is_zero, no-reply, 2016/08/24
- Re: [Qemu-devel] [PATCH 0/7] Improve buffer_is_zero, Dr. David Alan Gilbert, 2016/08/24