From mboxrd@z Thu Jan 1 00:00:00 1970 Return-Path: Received: from dpdk.org (dpdk.org [92.243.14.124]) by inbox.dpdk.org (Postfix) with ESMTP id 702FCA04C3 for ; Fri, 22 Nov 2019 15:42:10 +0100 (CET) Received: from [92.243.14.124] (localhost [127.0.0.1]) by dpdk.org (Postfix) with ESMTP id 6909D1C0B; Fri, 22 Nov 2019 15:42:10 +0100 (CET) Received: from us-smtp-delivery-1.mimecast.com (us-smtp-2.mimecast.com [205.139.110.61]) by dpdk.org (Postfix) with ESMTP id 4EA482C08 for ; Fri, 22 Nov 2019 15:42:09 +0100 (CET) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=redhat.com; s=mimecast20190719; t=1574433728; h=from:from:reply-to:subject:subject:date:date:message-id:message-id: to:to:cc:cc:mime-version:mime-version:content-type:content-type: content-transfer-encoding:content-transfer-encoding: in-reply-to:in-reply-to:references:references; bh=s0h5WR5rUgm/sMMGclWVdtCsRtVR3jV5YJpOjet/5hA=; b=LshozeI8+4zFpRmZQcrGVR7ofnt5y1X/7xCABmg124jtg0Xw6tL+k17EpRbrdtDcF9C4Pu oVMe2O/X3gUkqyLhA4N4VuPnvWRGc76WPLjOXbbv680bvupMTvg3iwHsw/2wUwo8mUeiEB BVIxEUvIgq4C1EKmbdku2KqLLUlt+2g= Received: from mimecast-mx01.redhat.com (mimecast-mx01.redhat.com [209.132.183.4]) (Using TLS) by relay.mimecast.com with ESMTP id us-mta-340-fxjh4uSKOg-rtsvFw-x2GQ-1; Fri, 22 Nov 2019 09:42:03 -0500 Received: from smtp.corp.redhat.com (int-mx02.intmail.prod.int.phx2.redhat.com [10.5.11.12]) (using TLSv1.2 with cipher AECDH-AES256-SHA (256/256 bits)) (No client certificate requested) by mimecast-mx01.redhat.com (Postfix) with ESMTPS id 2EF3F100550E; Fri, 22 Nov 2019 14:42:02 +0000 (UTC) Received: from rh.redhat.com (unknown [10.36.118.60]) by smtp.corp.redhat.com (Postfix) with ESMTP id 0921E8516; Fri, 22 Nov 2019 14:42:00 +0000 (UTC) From: Kevin Traynor To: Gavin Hu Cc: Ruifeng Wang , Steve Capper , dpdk stable Date: Fri, 22 Nov 2019 14:40:56 +0000 Message-Id: <20191122144131.21231-10-ktraynor@redhat.com> In-Reply-To: <20191122144131.21231-1-ktraynor@redhat.com> References: <20191122144131.21231-1-ktraynor@redhat.com> MIME-Version: 1.0 X-Scanned-By: MIMEDefang 2.79 on 10.5.11.12 X-MC-Unique: fxjh4uSKOg-rtsvFw-x2GQ-1 X-Mimecast-Spam-Score: 0 Content-Type: text/plain; charset=US-ASCII Content-Transfer-Encoding: quoted-printable Subject: [dpdk-stable] patch 'net/i40e: remove memory barrier from NEON Rx' has been queued to LTS release 18.11.6 X-BeenThere: stable@dpdk.org X-Mailman-Version: 2.1.15 Precedence: list List-Id: patches for DPDK stable branches List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , Errors-To: stable-bounces@dpdk.org Sender: "stable" Hi, FYI, your patch has been queued to LTS release 18.11.6 Note it hasn't been pushed to http://dpdk.org/browse/dpdk-stable yet. It will be pushed if I get no objections before 11/29/19. So please shout if anyone has objections. Also note that after the patch there's a diff of the upstream commit vs the patch applied to the branch. This will indicate if there was any rebasing needed to apply to the stable branch. If there were code changes for rebasi= ng (ie: not only metadata diffs), please double check that the rebase was correctly done. Queued patches are on a temporary branch at: https://github.com/kevintraynor/dpdk-stable-queue This queued commit can be viewed at: https://github.com/kevintraynor/dpdk-stable-queue/commit/8628a3a9bf8c8c1440= 62dc5ead06ac5be9061ff0 Thanks. Kevin. --- >From 8628a3a9bf8c8c144062dc5ead06ac5be9061ff0 Mon Sep 17 00:00:00 2001 From: Gavin Hu Date: Tue, 13 Aug 2019 18:43:30 +0800 Subject: [PATCH] net/i40e: remove memory barrier from NEON Rx [ upstream commit 78b50591c8e7ae3d010e8f4005e0e95c17800941 ] For x86, the descriptors needs to be loaded in order, so in between two descriptors loading, there is a compiler barrier in place.[1] For aarch64, a patch [2] is in place to survive with discontinuous DD bits, the barriers can be removed to take full advantage of out-of-order execution. 50% performance gain in the RFC2544 NDR test was measured on ThunderX2. 12.50% performance gain in the RFC2544 NDR test was measured on Ampere eMAG80 platform. [1] http://inbox.dpdk.org/users/039ED4275CED7440929022BC67E7061153D71548@ SHSMSX105.ccr.corp.intel.com/ [2] https://mails.dpdk.org/archives/stable/2017-October/003324.html Fixes: ae0eb310f253 ("net/i40e: implement vector PMD for ARM") Signed-off-by: Gavin Hu Reviewed-by: Ruifeng Wang Reviewed-by: Steve Capper --- drivers/net/i40e/i40e_rxtx_vec_neon.c | 1 - 1 file changed, 1 deletion(-) diff --git a/drivers/net/i40e/i40e_rxtx_vec_neon.c b/drivers/net/i40e/i40e_= rxtx_vec_neon.c index 83572ef84..5555e9b5c 100644 --- a/drivers/net/i40e/i40e_rxtx_vec_neon.c +++ b/drivers/net/i40e/i40e_rxtx_vec_neon.c @@ -286,5 +286,4 @@ _recv_raw_pkts_vec(struct i40e_rx_queue *rxq, struct rt= e_mbuf **rx_pkts, =09=09/* A.1 load 4 pkts desc */ =09=09descs[3] =3D vld1q_u64((uint64_t *)(rxdp + 3)); -=09=09rte_rmb(); =20 =09=09/* B.2 copy 2 mbuf point into rx_pkts */ --=20 2.21.0 --- Diff of the applied patch vs upstream commit (please double-check if non-= empty: --- --- -=092019-11-22 14:36:55.766493759 +0000 +++ 0010-net-i40e-remove-memory-barrier-from-NEON-Rx.patch=092019-11-22 14:= 36:55.153150226 +0000 @@ -1 +1 @@ -From 78b50591c8e7ae3d010e8f4005e0e95c17800941 Mon Sep 17 00:00:00 2001 +From 8628a3a9bf8c8c144062dc5ead06ac5be9061ff0 Mon Sep 17 00:00:00 2001 @@ -5,0 +6,2 @@ +[ upstream commit 78b50591c8e7ae3d010e8f4005e0e95c17800941 ] + @@ -21 +22,0 @@ -Cc: stable@dpdk.org