From b62c5f0df54512d8fd93dd28a2b482b2d2bad540 Mon Sep 17 00:00:00 2001 From: Marvin Liu Date: Wed, 6 May 2020 14:47:37 +0800 Subject: [PATCH] net/virtio: fix 32-bit build with clang 6 Clang 6.0.0 will undefine function _mm512_maskz_set1_epi64 on i686 target. Fix it by replacing the function with _mm512_set4_epi64 when doing 32-bit build. Warning message during build: ../drivers/net/virtio/virtio_rxtx_packed_avx.c:385:19: warning: implicit declaration of function '_mm512_maskz_set1_epi64' is invalid in C99 [-Wimplicit-function-declaration] Fixes: 77d66da83834 ("net/virtio: add vectorized packed ring Rx") Signed-off-by: Marvin Liu Reviewed-by: Maxime Coquelin --- drivers/net/virtio/virtio_rxtx_packed_avx.c | 10 ++++++++++ 1 file changed, 10 insertions(+) diff --git a/drivers/net/virtio/virtio_rxtx_packed_avx.c b/drivers/net/virtio/virtio_rxtx_packed_avx.c index d130d68bf2..6a82147258 100644 --- a/drivers/net/virtio/virtio_rxtx_packed_avx.c +++ b/drivers/net/virtio/virtio_rxtx_packed_avx.c @@ -365,7 +365,12 @@ virtqueue_dequeue_batch_packed_vec(struct virtnet_rx *rxvq, return -1; /* only care avail/used bits */ +#if defined(RTE_ARCH_I686) + __m512i v_mask = _mm512_set4_epi64(PACKED_FLAGS_MASK, 0x0, + PACKED_FLAGS_MASK, 0x0); +#else __m512i v_mask = _mm512_maskz_set1_epi64(0xaa, PACKED_FLAGS_MASK); +#endif desc_addr = &vq->vq_packed.ring.desc[id]; __m512i v_desc = _mm512_loadu_si512(desc_addr); @@ -373,7 +378,12 @@ virtqueue_dequeue_batch_packed_vec(struct virtnet_rx *rxvq, __m512i v_used_flag = _mm512_setzero_si512(); if (vq->vq_packed.used_wrap_counter) +#if defined(RTE_ARCH_I686) + v_used_flag = _mm512_set4_epi64(PACKED_FLAGS_MASK, 0x0, + PACKED_FLAGS_MASK, 0x0); +#else v_used_flag = _mm512_maskz_set1_epi64(0xaa, PACKED_FLAGS_MASK); +#endif /* Check all descs are used */ desc_stats = _mm512_cmpneq_epu64_mask(v_flag, v_used_flag); -- 2.20.1