d/numam-dpdk
1
0
Fork 0
Code Issues Pull Requests Projects Releases Wiki Activity

acl: fix build with gcc 5.4.0

Browse Source 
gcc 5.4 fails with:
../lib/librte_acl/acl_run_avx512x8.h: In function 'match_process_avx512x8':
../lib/librte_acl/acl_run_avx512x8.h:382:31: error:
pointer targets in passing argument 1 of '_mm256_mask_i32scatter_epi32'
differ in signedness [-Werror=pointer-sign]

Later gcc versions work fine, as for them parameter type was
changed to 'void *'.
Fixed by applying explicit cast for offending argument.

Bugzilla ID: 556
Fixes: b64c2295f7fc ("acl: add 256-bit AVX512 classify method")
Fixes: 45da22e42ec3 ("acl: add 512-bit AVX512 classify method")

Reported-by: Ali Alnubani <alialnu@nvidia.com>
Signed-off-by: Konstantin Ananyev <konstantin.ananyev@intel.com>
Tested-by: Ali Alnubani <alialnu@nvidia.com>
This commit is contained in:
Konstantin Ananyev 2020-10-15 12:53:56 +01:00 committed by David Marchand
parent 0c0d0d9df7
commit e0a1cd7a62
1 changed files with 2 additions and 2 deletions
Show Stats Download Patch File Download Diff File Expand all files Collapse all files

4
lib/librte_acl/acl_run_avx512_common.h
View File

@ -246,8 +246,8 @@ _F_(match_process)(struct acl_flow_avx512 *flow, uint32_t *fmsk,
tr_hi[0] = _M_I_(mask_mov_epi32)(tr_hi[0], rmsk[0], _SV_(trhi_idle));
/* save found match indexes */
_M_I_(mask_i32scatter_epi32)(flow->matches, rmsk[0], idx[0], res,
sizeof(flow->matches[0]));
_M_I_(mask_i32scatter_epi32)((void *)flow->matches, rmsk[0], idx[0],
res, sizeof(flow->matches[0]));
/* update masks and start new flows for matches */
n = update_flow_mask(flow, fmsk, rmsk);