From mboxrd@z Thu Jan  1 00:00:00 1970
Return-Path: <dev-bounces@dpdk.org>
Received: from mails.dpdk.org (mails.dpdk.org [217.70.189.124])
	by inbox.dpdk.org (Postfix) with ESMTP id 30B82A0548;
	Thu,  2 Jun 2022 20:42:04 +0200 (CEST)
Received: from [217.70.189.124] (localhost [127.0.0.1])
	by mails.dpdk.org (Postfix) with ESMTP id A8A3740691;
	Thu,  2 Jun 2022 20:42:04 +0200 (CEST)
Received: from mga01.intel.com (mga01.intel.com [192.55.52.88])
 by mails.dpdk.org (Postfix) with ESMTP id DB65E4021E;
 Thu,  2 Jun 2022 20:42:02 +0200 (CEST)
DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/simple;
 d=intel.com; i=@intel.com; q=dns/txt; s=Intel;
 t=1654195323; x=1685731323;
 h=message-id:date:subject:to:cc:references:from:
 in-reply-to:content-transfer-encoding:mime-version;
 bh=RCXFT3aDQVefm/HTTvp4vgNpnM7faWc9WYY6w5c/E3Q=;
 b=Imh5fg5DjZSzQ5R01M82kOY/00PBLWxQ3Jae68KwTY9m7N7oSWx8I7wI
 5j0l9kNWtdELXTZif70UD5Q5/0LyYhp4UlqkjVH6+6QqWsgNp4auDMze6
 Zf5iJcScneTbDlrBwPgPY/TJMG7oQ0m12P3S4kVSRwoB5D3Sfcr/EsXid
 URg0+X2F7/b2mkTE007jx6PVGGxMxJ98E9Rjvum+2144Q7qnE2oI3wY5L
 D9CFEi7RngV62ljQk/Gq5Y9zlvmLzYthGOsF7/SnXtoGi4WLgpA55f8/j
 r9zsNcDyCiBqHmkc7fmd5w5ZHrrgXxb0H0odRK5dlbNW9GHy1zX8GaHs+ Q==;
X-IronPort-AV: E=McAfee;i="6400,9594,10366"; a="301410639"
X-IronPort-AV: E=Sophos;i="5.91,272,1647327600"; d="scan'208";a="301410639"
Received: from fmsmga003.fm.intel.com ([10.253.24.29])
 by fmsmga101.fm.intel.com with ESMTP/TLS/ECDHE-RSA-AES256-GCM-SHA384;
 02 Jun 2022 11:42:01 -0700
X-ExtLoop1: 1
X-IronPort-AV: E=Sophos;i="5.91,272,1647327600"; d="scan'208";a="668114537"
Received: from orsmsx601.amr.corp.intel.com ([10.22.229.14])
 by FMSMGA003.fm.intel.com with ESMTP; 02 Jun 2022 11:42:01 -0700
Received: from orsmsx602.amr.corp.intel.com (10.22.229.15) by
 ORSMSX601.amr.corp.intel.com (10.22.229.14) with Microsoft SMTP Server
 (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id
 15.1.2308.27; Thu, 2 Jun 2022 11:42:01 -0700
Received: from orsedg603.ED.cps.intel.com (10.7.248.4) by
 orsmsx602.amr.corp.intel.com (10.22.229.15) with Microsoft SMTP Server
 (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id
 15.1.2308.27 via Frontend Transport; Thu, 2 Jun 2022 11:42:01 -0700
Received: from NAM10-DM6-obe.outbound.protection.outlook.com (104.47.58.100)
 by edgegateway.intel.com (134.134.137.100) with Microsoft SMTP Server
 (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id
 15.1.2308.27; Thu, 2 Jun 2022 11:42:00 -0700
ARC-Seal: i=1; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=none;
 b=NrHrSM6UdLX1k2GfQKuri5mhjCI0Q/b9k0STUQcYFAJWWVm20QQTKL1orG8JQ2MOuBpbEDCoEQsqgU9C71PUXAbbVBcsAdzABclPl8iSi5NPuJr6cAxr+D6HPsrNpgt/1DkuQSl54b2lw8TDuu5AKXjb8qhAsBg7181ZNsHk6HS+t9ADCqs3zmAmN/gbUvvhAV7IHzgJ8aL2Kt/GiUSYtwp0c0PqQNuAhvNEaYwu45zE+4Yu/ozvcf7UDWmbKBu4E3COTT3mfAP1haDktOSY2v1mMTONsKHIBC3BJ2nK43lukJArTSfc+Ios6JVcHfN+Q0qzVz08F31eau5CAIx6DA==
ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; 
 s=arcselector9901;
 h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-AntiSpam-MessageData-ChunkCount:X-MS-Exchange-AntiSpam-MessageData-0:X-MS-Exchange-AntiSpam-MessageData-1;
 bh=3W0+aJ9KRZaQHhIpJUdXUaT20bNlW1pC3gR/8D0bBok=;
 b=kuCR85zQ5uBLmjBDDbl3Yri7CE1EzWb7fJ3RtfgBsjwL7Yk4owheCWlv0i0H5NN7KI/wkDtTew8ZP77wW/CoJmyHucQ3zA3+7xy7EptwZD+pigIJtU8h9mpteFcgubkkRTsIrAo+z78Wr1S43gLnjgDWcmxV0sINor0vBt+6yl66rMCyxwD3w55jHnAaGm8pMlH5wzrVGwqZTfpwdl5N3Md6oRKljx7B68GCoA0mgvqJKPo9jU9I/s14RuH9WGEgDiYhmimAPsdNT95+2Fj3ihuv3XSfufnZKfE6HVxOL60NMKEvG66V1fwpzu7hTR7LHgCYfGB7PdiW5rm5VEu1Kw==
ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass
 smtp.mailfrom=intel.com; dmarc=pass action=none header.from=intel.com;
 dkim=pass header.d=intel.com; arc=none
Authentication-Results: dkim=none (message not signed)
 header.d=none;dmarc=none action=none header.from=intel.com;
Received: from SJ0PR11MB5772.namprd11.prod.outlook.com (2603:10b6:a03:422::8)
 by SA2PR11MB4827.namprd11.prod.outlook.com (2603:10b6:806:11f::19)
 with Microsoft SMTP Server (version=TLS1_2,
 cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.5314.13; Thu, 2 Jun
 2022 18:41:54 +0000
Received: from SJ0PR11MB5772.namprd11.prod.outlook.com
 ([fe80::64ab:a179:cce5:11d0]) by SJ0PR11MB5772.namprd11.prod.outlook.com
 ([fe80::64ab:a179:cce5:11d0%7]) with mapi id 15.20.5314.013; Thu, 2 Jun 2022
 18:41:54 +0000
Message-ID: <ccefe759-73db-9655-ed7a-0f4cc8b80556@intel.com>
Date: Thu, 2 Jun 2022 19:41:48 +0100
User-Agent: Mozilla/5.0 (Windows NT 10.0; Win64; x64; rv:91.0) Gecko/20100101
 Firefox/91.0 Thunderbird/91.9.1
Subject: Re: [PATCH 12/12] test/ipsec: fix build with GCC 12
Content-Language: en-US
To: David Marchand <david.marchand@redhat.com>, <dev@dpdk.org>
CC: <thomas@monjalon.net>, <ferruh.yigit@xilinx.com>, <stable@dpdk.org>,
 Konstantin Ananyev <konstantin.v.ananyev@yandex.ru>, Bernard Iremonger
 <bernard.iremonger@intel.com>
References: <20220518101657.1230416-1-david.marchand@redhat.com>
 <20220518101657.1230416-13-david.marchand@redhat.com>
From: "Medvedkin, Vladimir" <vladimir.medvedkin@intel.com>
In-Reply-To: <20220518101657.1230416-13-david.marchand@redhat.com>
Content-Type: text/plain; charset="UTF-8"; format=flowed
Content-Transfer-Encoding: 8bit
X-ClientProxiedBy: DB6P191CA0008.EURP191.PROD.OUTLOOK.COM (2603:10a6:6:28::18)
 To SJ0PR11MB5772.namprd11.prod.outlook.com
 (2603:10b6:a03:422::8)
MIME-Version: 1.0
X-MS-PublicTrafficType: Email
X-MS-Office365-Filtering-Correlation-Id: 4516d096-4908-490a-7d2d-08da44c79075
X-MS-TrafficTypeDiagnostic: SA2PR11MB4827:EE_
X-Microsoft-Antispam-PRVS: <SA2PR11MB4827FD5BBEAB20784DD835CF96DE9@SA2PR11MB4827.namprd11.prod.outlook.com>
X-MS-Exchange-SenderADCheck: 1
X-MS-Exchange-AntiSpam-Relay: 0
X-Microsoft-Antispam: BCL:0;
X-Microsoft-Antispam-Message-Info: ka7t/2t1KXe9gAFcx7YTCRcePD7bLFB/SfuU5OO9veDkYKENBJMajDy8din3SqQAQuHmNJBePV7O7Qqx8sO+lmJYn9cxERkntl+ojKe1nijm+uV3lfmvxAD9PIYu+EbO5or1c4KzJ8dhZSf5bQSM+sND74oqY/wjw3A/cp4JcYhm3hKj8Fm3k8IN7daHROUbPwL7kpG4RTAzUVzI8EPcQEbGOlBquDoYZk+rDUpwEsW7z+n8qpp27EFu3zxCCpgv4Hn2H1x4bbO8swNr1OWsD95kFnDW8zhr2fLZ8wNVQWasYSwbNGTxueinvfuOMQ6nuAHHD/6af5zCBlAZZQF3JNr0hFsH+MYlMOe7tsqL0dYAAUKCazZW/FpJybbGaF7+FQmDGhAibRvF1rZhtBn7r/1wWqRV8xu62hqQ35l+rynm7xGTqgZAE6o2ZyjbabwQUnAwgnv8jt41XJAqRpGq8eapawZeImkghGFlL0w23rc6BeXQc1B4vdTOsjeRfc9HnkzcfzAup/v7W3nuCIW0MOad0qKfFBBZBBZvmf+SzUeyUA0L7Pl8E/5V5Qb7PFRr0iIjn+D4ZcSxi8+t1MV7MHbL8XK1N1w+1Ms483iRK1roHC1ZbmBmFP/rp8vGMqiNE0N6VaYWUtIcEaL+WHS0LWESA1/RTLWUXsgd8S7UO4aDOSTZzMGR9RmzFj1h+Y1erZZlwJpkePLKpksdzWgY30pTq7X1byNtbWotUSm17kE=
X-Forefront-Antispam-Report: CIP:255.255.255.255; CTRY:; LANG:en; SCL:1; SRV:;
 IPV:NLI; SFV:NSPM; H:SJ0PR11MB5772.namprd11.prod.outlook.com; PTR:; CAT:NONE;
 SFS:(13230001)(366004)(66946007)(2616005)(316002)(26005)(54906003)(36756003)(38100700002)(66556008)(508600001)(5660300002)(31686004)(8936002)(2906002)(6666004)(4326008)(8676002)(82960400001)(6486002)(66476007)(6512007)(86362001)(107886003)(83380400001)(186003)(31696002)(53546011)(6506007)(43740500002)(45980500001);
 DIR:OUT; SFP:1102; 
X-MS-Exchange-AntiSpam-MessageData-ChunkCount: 1
X-MS-Exchange-AntiSpam-MessageData-0: =?utf-8?B?aDY5c3R4RzMzY25wZm90QzJBSHNBUFBwMEVIcU9KSjQ5VkZCckp2dkp4Mzll?=
 =?utf-8?B?Y0Frdko1N0s2TTlYSEZHM0xaMUlMYXVQeEp0ZS9sM1dnWkVGUzlkaEZBSVE2?=
 =?utf-8?B?N1BFV1R6L2xOYzE1S2tZVXJkTmZrUXN2M2xJenlFREZNZmlrWDBTcS8yYnNY?=
 =?utf-8?B?bU5FWXcyYnk3WFBKaExvVG5GdzEyeWdHbTRvLzhXZFB5RE4zblVibkhGWno5?=
 =?utf-8?B?UzNuMWlVSmFCcEhwRXQ2bURvWTlvRTNoUVhoOXJRQU1ZSjdzVTZsdHZQc0c5?=
 =?utf-8?B?NFJBLzdVN3YvdTZneFhUa0VMNWltRjJKaU9kdHpoZnZmUmpJZ1hONXhaZWJr?=
 =?utf-8?B?aXdSbGZIamk1LytUN21SRlk0SzFiU01RSGpUNnNiMHNYWWkwOFRLRlJueURn?=
 =?utf-8?B?Mm0ySFRaRUtsWTg3SmFUd2o4NmNNZ3h4RWgrTk4zT3IxNnk2Qmh3ejJwcWpt?=
 =?utf-8?B?SnY4SER5Z2plZGlRbXVmOWoxMTE2UW5ndnRBZm1qR3B6M3NMdzVPSWIrZzBS?=
 =?utf-8?B?eXBTd2luZDV2UlVFVmcrOVhWUS9qaWIrYUlWU09iVHpkd2l3bDBMZU1qTGJm?=
 =?utf-8?B?UnhyQ0hsNUZ5RElvVWZ2OW80ditaaGdjYzRDNHNycWR3RGlRaEJ3SHlmOXFX?=
 =?utf-8?B?SFphUUQrWHZJN1NXSFZmY0NFc3loVDJIQnJwYmQzTm14TG1ySmNKNFo5TTRy?=
 =?utf-8?B?RFhMNlUzWGNCYkx2c2lheWZYbW9wMTQwdVV4dEdsZDhYckphYi9iMURDbmY1?=
 =?utf-8?B?TGpKMy9mdDJpZjVKd3ZhK1hjamh6dVI0elU2amxyQnNsOXhwMFJDb0w5ODdQ?=
 =?utf-8?B?MlhveUlCQmZjc1EzTnpkY3NSbjUyT1pMaUoyUnMxQm1yVHBESHpkYythRTVV?=
 =?utf-8?B?KzhVS2UxMnU2aVVBcEhNbFJxaUg3Nkg5dHpGeVdoczZvMGJyU25LaWZJQkk5?=
 =?utf-8?B?WlVFT2EwNTZxUU4rZHdoeGRIQ3RvTWRHU1d4NFJFQ1NYQnBlZ0p6MVZDaThN?=
 =?utf-8?B?QzhiOXBRb01PS08rS3NQUmV4RE81ZkJjeGJJV0xuNE1mKzRPdkprNGpOZlEy?=
 =?utf-8?B?Q250RmxZS0ZUeU1aOGNkY2I1NDdWOVFrTlRyOG9JS2IrNXh1WEtBaXo5NFcx?=
 =?utf-8?B?eUwySkpScFluRXI5emxPcUFEeVYrZ1VpVnQvTjdFeUd6dHA2amppQWk3M3M4?=
 =?utf-8?B?eStHODFwYWFvM3ZEVkZXWHRjMUpqZm9OYlFwa0R5Y1BxOWgrbWxKSktDd2E5?=
 =?utf-8?B?ZjRtQUVRcjc1Ykx3Wjd4dVpadGVBMDFIM1NRVEdrS3M0dXhpTkNFSzBTY0JY?=
 =?utf-8?B?dVJmeVNoaWxmQ2o0blJHOGdrMWlmVklCbzNIdDRreHc4bG9CUWthTEl6ZE5F?=
 =?utf-8?B?OHd5Z0dhcEhCS0pEb3N4Rm5KcDJLZGVRLzFZVDE4aXNNeEZBRy9mb1pJT0tU?=
 =?utf-8?B?YTlabDF2Lzl0bTBqb1JwcmVOd1ZNekpudHBzdU96dUZwK3I1VkJ3Nzhnd0da?=
 =?utf-8?B?ek02bXFuV2hiU3JLd09TVVRCTy9CWU85UWFFYnlLSVRjRHRzS3daVTNheXZU?=
 =?utf-8?B?QnovdkRncWpTUm4yU213K25WVE0zK1hoT3RpdnBOTVE5SkRpakQ1MGNhMlBn?=
 =?utf-8?B?ZmFySUwza2FDODhGSnR3czVHN2FKMmErb1ZxUVJDOHZ5MzZPbHFQdlJOOFVU?=
 =?utf-8?B?VVVuZkdRa0ZyRDNDajFFTWpnNE01ZzlmWHVYcGljajNvL2UvQ1RYaW52MUcx?=
 =?utf-8?B?eU40SERmZGhPR2Vrdm4za3FhUlBGd1FScFFJVUpDTmowUWFNSmo4cXdnYXJz?=
 =?utf-8?B?ajVBTnBPRTZGMjVkY2lwWUk1WmY1Y0E3amhyeFpmdE1XNkxJUDNpYlhaano0?=
 =?utf-8?B?VFVNU2UwSmRtQ0NsOXVyaTZQTGV3RUoyV0VUamlTV3VieEd0WmdSdUFHYjlO?=
 =?utf-8?B?V1kxRXhxcEFiY0R5R2k3RWo3VGRiZHlOZk5QUHp4Z0F2RTVIdGpnQTFzMXVF?=
 =?utf-8?B?czRhNlJzZnlEdGw0TTIxbzhzYnFtSi9SR1FYWVR3aWQ3U1NEelhaU2Y3ZDJv?=
 =?utf-8?B?K2RFU244RnRXak5pQXNUVzYwc1NoNUlXNWVKYWFneElVaHY2Q2Z4OW44a1Rt?=
 =?utf-8?B?dVl5ZngwQWVkUW50M21qK0JOQnRrUW9KYlhrWHlOSENkS3hrMW5ESng3R1Qx?=
 =?utf-8?B?MjNaN01zR2w1andvNkUrRUlWSE5vYjQ0YXFTcGFEK014YzdYRmJ4UU5TcVhy?=
 =?utf-8?B?SDN6ZmtzVitLL2tpOGZKWkIxS1NLelhtOVQzck5RbDRzN2JYd2QvTnV5MzVG?=
 =?utf-8?B?Y2xNaFdlT3JteWl6WDdubUx1UkdyZmhuakx3VVM0eVVJOSt5S2FIdnphY1Jy?=
 =?utf-8?Q?RGpqDpRKGUfLMq6A=3D?=
X-MS-Exchange-CrossTenant-Network-Message-Id: 4516d096-4908-490a-7d2d-08da44c79075
X-MS-Exchange-CrossTenant-AuthSource: SJ0PR11MB5772.namprd11.prod.outlook.com
X-MS-Exchange-CrossTenant-AuthAs: Internal
X-MS-Exchange-CrossTenant-OriginalArrivalTime: 02 Jun 2022 18:41:54.3363 (UTC)
X-MS-Exchange-CrossTenant-FromEntityHeader: Hosted
X-MS-Exchange-CrossTenant-Id: 46c98d88-e344-4ed4-8496-4ed7712e255d
X-MS-Exchange-CrossTenant-MailboxType: HOSTED
X-MS-Exchange-CrossTenant-UserPrincipalName: 8SoxqBbHyJlflDsLTMXkGWFjzOfgPVqYz35kiRu5NEvXD6MAebahKE8kwQWCZEaIc1GBsxx3QkczID1/mbjHzB5dgtmUKkJThGeqH4jWSdY=
X-MS-Exchange-Transport-CrossTenantHeadersStamped: SA2PR11MB4827
X-OriginatorOrg: intel.com
X-BeenThere: dev@dpdk.org
X-Mailman-Version: 2.1.29
Precedence: list
List-Id: DPDK patches and discussions <dev.dpdk.org>
List-Unsubscribe: <https://mails.dpdk.org/options/dev>,
 <mailto:dev-request@dpdk.org?subject=unsubscribe>
List-Archive: <http://mails.dpdk.org/archives/dev/>
List-Post: <mailto:dev@dpdk.org>
List-Help: <mailto:dev-request@dpdk.org?subject=help>
List-Subscribe: <https://mails.dpdk.org/listinfo/dev>,
 <mailto:dev-request@dpdk.org?subject=subscribe>
Errors-To: dev-bounces@dpdk.org

Hi David,

On 18/05/2022 11:16, David Marchand wrote:
> GCC 12 raises the following warning:
> 
> In function ‘_mm256_loadu_si256’,
>      inlined from ‘rte_mov32’ at
>          ../lib/eal/x86/include/rte_memcpy.h:319:9,
>      inlined from ‘rte_mov128’ at
>          ../lib/eal/x86/include/rte_memcpy.h:344:2,
>      inlined from ‘rte_memcpy_generic’ at
>          ../lib/eal/x86/include/rte_memcpy.h:438:4,
>      inlined from ‘rte_memcpy’ at
>          ../lib/eal/x86/include/rte_memcpy.h:882:10,
>      inlined from ‘setup_test_string.constprop’ at
>          ../app/test/test_ipsec.c:572:4:
> /usr/lib/gcc/x86_64-redhat-linux/12/include/avxintrin.h:929:10: error:
>      array subscript ‘__m256i_u[3]’ is partly outside array bounds of
>      ‘const char[108]’ [-Werror=array-bounds]
>    929 |   return *__P;
>        |          ^~~~
> ../app/test/test_ipsec.c: In function ‘setup_test_string.constprop’:
> ../app/test/test_ipsec.c:539:12: note: at offset 96 into object
>      ‘null_plain_data’ of size 108
>    539 | const char null_plain_data[] =
>        |            ^~~~~~~~~~~~~~~
> 
> Split copy request into copies of string lengths and remove unused
> blocksize.
> 
> Cc: stable@dpdk.org
> 
> Signed-off-by: David Marchand <david.marchand@redhat.com>
> ---
>   app/test/test_ipsec.c | 48 ++++++++++++++++++++++++++-----------------
>   1 file changed, 29 insertions(+), 19 deletions(-)
> 
> diff --git a/app/test/test_ipsec.c b/app/test/test_ipsec.c
> index 8da025bf66..d7455fd021 100644
> --- a/app/test/test_ipsec.c
> +++ b/app/test/test_ipsec.c
> @@ -554,24 +554,28 @@ struct rte_ipv4_hdr ipv4_outer  = {
>   };
>   
>   static struct rte_mbuf *
> -setup_test_string(struct rte_mempool *mpool,
> -		const char *string, size_t len, uint8_t blocksize)
> +setup_test_string(struct rte_mempool *mpool, const char *string,
> +	size_t string_len, size_t len)
>   {
>   	struct rte_mbuf *m = rte_pktmbuf_alloc(mpool);
> -	size_t t_len = len - (blocksize ? (len % blocksize) : 0);
>   
>   	if (m) {
>   		memset(m->buf_addr, 0, m->buf_len);
> -		char *dst = rte_pktmbuf_append(m, t_len);
> +		char *dst = rte_pktmbuf_append(m, len);
>   
>   		if (!dst) {
>   			rte_pktmbuf_free(m);
>   			return NULL;
>   		}
> -		if (string != NULL)
> -			rte_memcpy(dst, string, t_len);
> -		else
> -			memset(dst, 0, t_len);
> +		if (string != NULL) {
> +			size_t off;
> +
> +			for (off = 0; off + string_len < len; off += string_len)

I think it should be off + string_len <= len here, because otherwise, if 
len is a multiple of string_len, the last ret_memcpy (after this loop) 
will copy 0 bytes.

> +				rte_memcpy(&dst[off], string, string_len);
> +			rte_memcpy(&dst[off], string, len % string_len);
> +		} else {
> +			memset(dst, 0, len);
> +		}
>   	}
>   
>   	return m;
> @@ -1365,7 +1369,8 @@ test_ipsec_crypto_outb_burst_null_null(int i)
>   	/* Generate input mbuf data */
>   	for (j = 0; j < num_pkts && rc == 0; j++) {
>   		ut_params->ibuf[j] = setup_test_string(ts_params->mbuf_pool,
> -			null_plain_data, test_cfg[i].pkt_sz, 0);
> +			null_plain_data, sizeof(null_plain_data),
> +			test_cfg[i].pkt_sz);
>   		if (ut_params->ibuf[j] == NULL)
>   			rc = TEST_FAILED;
>   		else {
> @@ -1483,7 +1488,8 @@ test_ipsec_inline_crypto_inb_burst_null_null(int i)
>   			/* Generate test mbuf data */
>   			ut_params->obuf[j] = setup_test_string(
>   				ts_params->mbuf_pool,
> -				null_plain_data, test_cfg[i].pkt_sz, 0);
> +				null_plain_data, sizeof(null_plain_data),
> +				test_cfg[i].pkt_sz);
>   			if (ut_params->obuf[j] == NULL)
>   				rc = TEST_FAILED;
>   		}
> @@ -1551,16 +1557,17 @@ test_ipsec_inline_proto_inb_burst_null_null(int i)
>   
>   	/* Generate inbound mbuf data */
>   	for (j = 0; j < num_pkts && rc == 0; j++) {
> -		ut_params->ibuf[j] = setup_test_string(
> -			ts_params->mbuf_pool,
> -			null_plain_data, test_cfg[i].pkt_sz, 0);
> +		ut_params->ibuf[j] = setup_test_string(ts_params->mbuf_pool,
> +			null_plain_data, sizeof(null_plain_data),
> +			test_cfg[i].pkt_sz);
>   		if (ut_params->ibuf[j] == NULL)
>   			rc = TEST_FAILED;
>   		else {
>   			/* Generate test mbuf data */
>   			ut_params->obuf[j] = setup_test_string(
>   				ts_params->mbuf_pool,
> -				null_plain_data, test_cfg[i].pkt_sz, 0);
> +				null_plain_data, sizeof(null_plain_data),
> +				test_cfg[i].pkt_sz);
>   			if (ut_params->obuf[j] == NULL)
>   				rc = TEST_FAILED;
>   		}
> @@ -1660,7 +1667,8 @@ test_ipsec_inline_crypto_outb_burst_null_null(int i)
>   	/* Generate test mbuf data */
>   	for (j = 0; j < num_pkts && rc == 0; j++) {
>   		ut_params->ibuf[j] = setup_test_string(ts_params->mbuf_pool,
> -			null_plain_data, test_cfg[i].pkt_sz, 0);
> +			null_plain_data, sizeof(null_plain_data),
> +			test_cfg[i].pkt_sz);
>   		if (ut_params->ibuf[0] == NULL)
>   			rc = TEST_FAILED;
>   
> @@ -1738,15 +1746,16 @@ test_ipsec_inline_proto_outb_burst_null_null(int i)
>   	/* Generate test mbuf data */
>   	for (j = 0; j < num_pkts && rc == 0; j++) {
>   		ut_params->ibuf[j] = setup_test_string(ts_params->mbuf_pool,
> -			null_plain_data, test_cfg[i].pkt_sz, 0);
> +			null_plain_data, sizeof(null_plain_data),
> +			test_cfg[i].pkt_sz);
>   		if (ut_params->ibuf[0] == NULL)
>   			rc = TEST_FAILED;
>   
>   		if (rc == 0) {
>   			/* Generate test tunneled mbuf data for comparison */
>   			ut_params->obuf[j] = setup_test_string(
> -					ts_params->mbuf_pool,
> -					null_plain_data, test_cfg[i].pkt_sz, 0);
> +				ts_params->mbuf_pool, null_plain_data,
> +				sizeof(null_plain_data), test_cfg[i].pkt_sz);
>   			if (ut_params->obuf[j] == NULL)
>   				rc = TEST_FAILED;
>   		}
> @@ -1815,7 +1824,8 @@ test_ipsec_lksd_proto_inb_burst_null_null(int i)
>   	for (j = 0; j < num_pkts && rc == 0; j++) {
>   		/* packet with sequence number 0 is invalid */
>   		ut_params->ibuf[j] = setup_test_string(ts_params->mbuf_pool,
> -			null_encrypted_data, test_cfg[i].pkt_sz, 0);
> +			null_encrypted_data, sizeof(null_encrypted_data),
> +			 test_cfg[i].pkt_sz);
>   		if (ut_params->ibuf[j] == NULL)
>   			rc = TEST_FAILED;
>   	}

-- 
Regards,
Vladimir