From mboxrd@z Thu Jan 1 00:00:00 1970 Received: from eggs.gnu.org ([2001:4830:134:3::10]:40983) by lists.gnu.org with esmtp (Exim 4.71) (envelope-from ) id 1bjqIo-0003NA-3W for qemu-devel@nongnu.org; Tue, 13 Sep 2016 12:11:22 -0400 Received: from Debian-exim by eggs.gnu.org with spam-scanned (Exim 4.71) (envelope-from ) id 1bjqIi-00020V-B1 for qemu-devel@nongnu.org; Tue, 13 Sep 2016 12:11:17 -0400 Received: from mail-wm0-f65.google.com ([74.125.82.65]:33922) by eggs.gnu.org with esmtp (Exim 4.71) (envelope-from ) id 1bjqIi-000209-5p for qemu-devel@nongnu.org; Tue, 13 Sep 2016 12:11:12 -0400 Received: by mail-wm0-f65.google.com with SMTP id g141so8003809wmd.1 for ; Tue, 13 Sep 2016 09:11:12 -0700 (PDT) Sender: Paolo Bonzini From: Paolo Bonzini Date: Tue, 13 Sep 2016 18:09:57 +0200 Message-Id: <1473783005-113609-3-git-send-email-pbonzini@redhat.com> In-Reply-To: <1473783005-113609-1-git-send-email-pbonzini@redhat.com> References: <1473783005-113609-1-git-send-email-pbonzini@redhat.com> Subject: [Qemu-devel] [PATCH 02/10] cutils: Remove SPLAT macro List-Id: List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , To: qemu-devel@nongnu.org Cc: rth@twiddle.net From: Richard Henderson This is unused and complicates the vector interface. Signed-off-by: Richard Henderson Message-Id: <1472496380-19706-3-git-send-email-rth@twiddle.net> Signed-off-by: Paolo Bonzini --- 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 #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 #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