From mboxrd@z Thu Jan 1 00:00:00 1970 Return-Path: Received: from mails.dpdk.org (mails.dpdk.org [217.70.189.124]) by inbox.dpdk.org (Postfix) with ESMTP id ED237A0093; Mon, 7 Nov 2022 13:00:46 +0100 (CET) Received: from [217.70.189.124] (localhost [127.0.0.1]) by mails.dpdk.org (Postfix) with ESMTP id D63DB40156; Mon, 7 Nov 2022 13:00:46 +0100 (CET) Received: from mail-yb1-f179.google.com (mail-yb1-f179.google.com [209.85.219.179]) by mails.dpdk.org (Postfix) with ESMTP id 976C840151 for ; Mon, 7 Nov 2022 13:00:45 +0100 (CET) Received: by mail-yb1-f179.google.com with SMTP id k13so9465470ybk.2 for ; Mon, 07 Nov 2022 04:00:45 -0800 (PST) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=20210112; h=cc:to:subject:message-id:date:from:in-reply-to:references :mime-version:from:to:cc:subject:date:message-id:reply-to; bh=Tc1l5uT8dNhdmRIRCYwETuk0M3nMZnLYDpwTtISfBZ4=; b=cBQhgcKhLD4M44SAT4yrKphgAuIB4rkAbfx7U1gkjQVWNrtSChH96U79RnYqv9kNHz ImWvwHaZv6wQlUb8xowyT8jHtoMrCmSnxYzktzlE+Q1uZYBPJF3xodBg2eMbCiQo0w5t YoV2e5wi7yvZBBdTxTx5/PY+TPnsw82XuN66YG3cavh8BrhJT4GcbX+BOFC6LVlVUEyt 8OxW0fONWKRqd785mxYduysHbOvkmtQeyykmi4oqr7j9+5wrPQ774n9kRB5W1QiLXHIq TGT+HTX3gl4XUSGBV47xP36saxiUe1NNaKc1T+n3fcPPv8JE/A8Q6lvW5WBHjqZ4Exon cBBg== X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=1e100.net; s=20210112; h=cc:to:subject:message-id:date:from:in-reply-to:references :mime-version:x-gm-message-state:from:to:cc:subject:date:message-id :reply-to; bh=Tc1l5uT8dNhdmRIRCYwETuk0M3nMZnLYDpwTtISfBZ4=; b=KgzNWzawLKbZcOV4mn6SMdAyNmDFIlcVC1YxDtWxBUPYrukotdemvsg9tCctZVSzMg FnBrcUzPcJCHOpPR5pNm7FogJ/E8eXfw4q7dARF3k5p8JIp339Gud7KVK2c+GpHH9g1J 8hxNtGKe6smBBxU4VmBu5avHfKZ02a1jbkporETTYzWvmZ3WdQCdAv9pvdt5LfTeBeoT tza7AIAacgjbhEtOsqe/HExAF4rEWlRZkSw+oQIfaQRjvs27pFcvgNMKK3deHkDQXUk7 JUIjN3kv0TsGDuwfXfEZQc8lImMNrcTNhHQzmTY92xK4v7M6nOv4roDmt4dSwFyY5rHd uAjQ== X-Gm-Message-State: ANoB5pk6X4t7IKLI+zgAC3bOQnFkcc1xyKefbuZy1K56qUl1k1xXlDZ6 vmTXS7EcfgW54H6w1psorRP6wQ2OTzB1izO3bzk= X-Google-Smtp-Source: AA0mqf6P3gJJp5iUBo/ZwpNvNYrV/XEefmuRL+Oq+p3z6zQ5r3J2+djot5BNpYUIuWyd0R3sJ6eX5MtE72g4yYuOrnE= X-Received: by 2002:a25:8b8f:0:b0:6d6:acf:193c with SMTP id j15-20020a258b8f000000b006d60acf193cmr7493233ybl.524.1667822444805; Mon, 07 Nov 2022 04:00:44 -0800 (PST) MIME-Version: 1.0 References: <20221025154653.10482-1-pbhagavatula@marvell.com> <20221025161129.15933-1-pbhagavatula@marvell.com> In-Reply-To: <20221025161129.15933-1-pbhagavatula@marvell.com> From: Jerin Jacob Date: Mon, 7 Nov 2022 17:30:18 +0530 Message-ID: Subject: Re: [PATCH v2] event/cnxk: fix incorrect mbuf offset calculation To: pbhagavatula@marvell.com Cc: jerinj@marvell.com, Nithin Dabilpuram , Kiran Kumar K , Sunil Kumar Kori , Satha Rao , dev@dpdk.org Content-Type: text/plain; charset="UTF-8" X-BeenThere: dev@dpdk.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: DPDK patches and discussions List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , Errors-To: dev-bounces@dpdk.org On Tue, Oct 25, 2022 at 9:41 PM wrote: > > From: Pavan Nikhilesh > > Fix incorrect mbuf offset calculation when HEADROOM exceeds 128B > while processing event vectors. > > Fixes: 7fbbc981d54f("event/cnxk: support vectorized Rx event fast path") Cc: stable@dpdk.org Applied to dpdk-next-net-eventdev/for-main. Thanks > > Signed-off-by: Pavan Nikhilesh > --- > v2 Changes: > - Remove internal Change-Id. > > drivers/net/cnxk/cn10k_rx.h | 8 +++++--- > 1 file changed, 5 insertions(+), 3 deletions(-) > > diff --git a/drivers/net/cnxk/cn10k_rx.h b/drivers/net/cnxk/cn10k_rx.h > index 46488d442e..f562a75245 100644 > --- a/drivers/net/cnxk/cn10k_rx.h > +++ b/drivers/net/cnxk/cn10k_rx.h > @@ -1201,9 +1201,11 @@ cn10k_nix_recv_pkts_vector(void *args, struct rte_mbuf **mbufs, uint16_t pkts, > mbuf23 = vqsubq_u64(mbuf23, data_off); > } else { > mbuf01 = > - vsubq_u64(vld1q_u64((uint64_t *)cq0), data_off); > - mbuf23 = vsubq_u64(vld1q_u64((uint64_t *)(cq0 + 16)), > - data_off); > + vsubq_u64(vld1q_u64((uint64_t *)cq0), > + vdupq_n_u64(sizeof(struct rte_mbuf))); > + mbuf23 = > + vsubq_u64(vld1q_u64((uint64_t *)(cq0 + 16)), > + vdupq_n_u64(sizeof(struct rte_mbuf))); > } > > /* Move mbufs to scalar registers for future use */ > -- > 2.25.1 >