NetBSD Problem Report #59093
From o.vd.linden@quicknet.nl Sat Feb 22 11:29:48 2025
Return-Path: <o.vd.linden@quicknet.nl>
Received: from mail.netbsd.org (mail.netbsd.org [199.233.217.200])
(using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits)
key-exchange X25519 server-signature RSA-PSS (2048 bits)
client-signature RSA-PSS (2048 bits))
(Client CN "mail.NetBSD.org", Issuer "mail.NetBSD.org CA" (not verified))
by mollari.NetBSD.org (Postfix) with ESMTPS id 8F7061A923F
for <gnats-bugs@gnats.NetBSD.org>; Sat, 22 Feb 2025 11:29:48 +0000 (UTC)
Message-Id: <Z7muhxDwEknhpul3@sheep>
Date: Sat, 22 Feb 2025 12:01:27 +0100
From: Onno van der Linden <o.vd.linden@quicknet.nl>
Reply-To:
To: gnats-bugs@netbsd.org
Subject: compile errors for userland on amd64 with gcc and -march=nativ
>Number: 59093
>Notify-List: riastradh@NetBSD.org, mrg@NetBSD.org, christos@NetBSD.org
>Category: bin
>Synopsis: Subject: compile errors for userland on amd64 with gcc and -march=native
>Confidential: no
>Severity: non-critical
>Priority: low
>Responsible: bin-bug-people
>State: feedback
>Class: sw-bug
>Submitter-Id: net
>Arrival-Date: Sat Feb 22 11:30:01 +0000 2025
>Closed-Date:
>Last-Modified: Fri Feb 28 16:10:01 +0000 2025
>Originator: Onno van der Linden <o.vd.linden@quicknet.nl>
>Release: NetBSD 10.99.12
>Organization:
>Environment:
System: NetBSD sheep 10.99.12 NetBSD 10.99.12 (SHEEP) #0: Sun Feb 16 23:42:11 CET 2025 onno@sheep:/usr/src/sys/arch/amd64/compile/SHEEP amd64
Architecture: x86_64
Machine: amd64
>Description:
compiling userland on amd64 with gcc and the -march=native compiler option
results in compile errors in libm for libm/ld80/e_lgammal_r.c and in zstd
for most of the files in lib.
>How-To-Repeat:
Add CPUFLAGS=-march=native in /etc/mk.conf on a amd64 machine and compile
libm and zstd
>Fix:
Fix for lgammal_r.c
--- /usr/src/lib/libm/ld80/e_lgammal_r.c.orig 2025-02-21 19:19:42.227612980 +0100
+++ /usr/src/lib/libm/ld80/e_lgammal_r.c 2025-02-21 19:28:51.125599005 +0100
@@ -242,7 +242,7 @@
long double
lgammal_r(long double x, int *signgamp)
{
- long double nadj,p,p1,p2,q,r,t,w,y,z;
+ long double nadj = 0, p,p1,p2,q,r,t,w,y,z;
uint64_t lx;
int i;
uint16_t hx,ix;
Fix for zstd:
--- /usr/src/external/bsd/zstd/dist/lib/common/bitstream.h 2025-02-22 11:30:31.613540814 +0100
+++ /usr/src/external/bsd/zstd/dist/lib/common/bitstream.h.new 2025-02-22 11:20:41.986663437 +0100
@@ -38,7 +38,10 @@
=========================================*/
#ifndef ZSTD_NO_INTRINSICS
# if (defined(__BMI__) || defined(__BMI2__)) && defined(__GNUC__)
+#pragma GCC diagnostic push
+#pragma GCC diagnostic ignored "-Wcast-qual"
# include <immintrin.h> /* support for bextr (experimental)/bzhi */
+#pragma GCC diagnostic pop
# elif defined(__ICCARM__)
# include <intrinsics.h>
# endif
Alternative fix for zstd is to fix the gcc headers and make them look like
the llvm headers by adding const to several type casts. This doesn't work
for _mm256_stream_load_si256 because __builtin_ia32_movntdqa256 has
a non-const argument. Possible fixes in that case are #pragma, __UNCONST or
changing the argument of __builtin_ia32_movntdqa256 to a const. I opted for
the first one.
--- /usr/src/external/gpl3/gcc/dist/gcc/config/i386/avx2intrin.h 2023-07-30 10:11:55.590996415 +0200
+++ /usr/src/external/gpl3/gcc/dist/gcc/config/i386/avx2intrin.h.new 2025-02-22 11:07:03.868781092 +0100
@@ -919,7 +919,14 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_stream_load_si256 (__m256i const *__X)
{
+#ifdef __GNUC__
+#pragma GCC diagnostic push
+#pragma GCC diagnostic ignored "-Wcast-qual"
+#endif
return (__m256i) __builtin_ia32_movntdqa256 ((__v4di *) __X);
+#ifdef __GNUC__
+#pragma GCC diagnostic pop
+#endif
}
extern __inline __m128
--- /usr/src/external/gpl3/gcc/dist/gcc/config/i386/avx512bwintrin.h 2023-07-30 10:11:55.611241653 +0200
+++ /usr/src/external/gpl3/gcc/dist/gcc/config/i386/avx512bwintrin.h.new 2025-02-22 11:07:03.873160880 +0100
@@ -309,7 +309,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_loadu_epi16 (void const *__P)
{
- return (__m512i) (*(__v32hi_u *) __P);
+ return (__m512i) (*(const __v32hi_u *) __P);
}
extern __inline __m512i
@@ -402,7 +402,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_loadu_epi8 (void const *__P)
{
- return (__m512i) (*(__v64qi_u *) __P);
+ return (__m512i) (*(const __v64qi_u *) __P);
}
extern __inline __m512i
--- /usr/src/external/gpl3/gcc/dist/gcc/config/i386/avx512fintrin.h 2023-07-30 10:11:55.722942211 +0200
+++ /usr/src/external/gpl3/gcc/dist/gcc/config/i386/avx512fintrin.h.new 2025-02-22 11:07:03.878562205 +0100
@@ -387,7 +387,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_load_pd (void const *__P)
{
- return *(__m512d *) __P;
+ return *(const __m512d *) __P;
}
extern __inline __m512d
@@ -428,7 +428,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_load_ps (void const *__P)
{
- return *(__m512 *) __P;
+ return *(const __m512 *) __P;
}
extern __inline __m512
@@ -488,7 +488,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_load_epi64 (void const *__P)
{
- return *(__m512i *) __P;
+ return *(const __m512i *) __P;
}
extern __inline __m512i
@@ -548,14 +548,14 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_load_si512 (void const *__P)
{
- return *(__m512i *) __P;
+ return *(const __m512i *) __P;
}
extern __inline __m512i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_load_epi32 (void const *__P)
{
- return *(__m512i *) __P;
+ return *(const __m512i *) __P;
}
extern __inline __m512i
@@ -6298,7 +6298,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_loadu_pd (void const *__P)
{
- return *(__m512d_u *)__P;
+ return *(const __m512d_u *)__P;
}
extern __inline __m512d
@@ -6339,7 +6339,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_loadu_ps (void const *__P)
{
- return *(__m512_u *)__P;
+ return *(const __m512_u *)__P;
}
extern __inline __m512
@@ -6457,7 +6457,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_loadu_epi64 (void const *__P)
{
- return *(__m512i_u *) __P;
+ return *(const __m512i_u *) __P;
}
extern __inline __m512i
@@ -6498,14 +6498,14 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_loadu_si512 (void const *__P)
{
- return *(__m512i_u *)__P;
+ return *(const __m512i_u *)__P;
}
extern __inline __m512i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_loadu_epi32 (void const *__P)
{
- return *(__m512i_u *) __P;
+ return *(const __m512i_u *) __P;
}
extern __inline __m512i
--- /usr/src/external/gpl3/gcc/dist/gcc/config/i386/avx512vlbwintrin.h 2023-07-30 10:11:56.697259945 +0200
+++ /usr/src/external/gpl3/gcc/dist/gcc/config/i386/avx512vlbwintrin.h.new 2025-02-22 11:07:03.882921173 +0100
@@ -118,7 +118,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_loadu_epi16 (void const *__P)
{
- return (__m256i) (*(__v16hi_u *) __P);
+ return (__m256i) (*(const __v16hi_u *) __P);
}
extern __inline __m256i
@@ -144,7 +144,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_loadu_epi16 (void const *__P)
{
- return (__m128i) (*(__v8hi_u *) __P);
+ return (__m128i) (*(const __v8hi_u *) __P);
}
extern __inline __m128i
@@ -209,7 +209,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_loadu_epi8 (void const *__P)
{
- return (__m256i) (*(__v32qi_u *) __P);
+ return (__m256i) (*(const __v32qi_u *) __P);
}
extern __inline __m256i
@@ -235,7 +235,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_loadu_epi8 (void const *__P)
{
- return (__m128i) (*(__v16qi_u *) __P);
+ return (__m128i) (*(const __v16qi_u *) __P);
}
extern __inline __m128i
--- /usr/src/external/gpl3/gcc/dist/gcc/config/i386/avx512vlintrin.h 2023-07-30 10:11:56.809195380 +0200
+++ /usr/src/external/gpl3/gcc/dist/gcc/config/i386/avx512vlintrin.h.new 2025-02-22 11:07:03.888239581 +0100
@@ -87,7 +87,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_load_pd (__m256d __W, __mmask8 __U, void const *__P)
{
- return (__m256d) __builtin_ia32_loadapd256_mask ((__v4df *) __P,
+ return (__m256d) __builtin_ia32_loadapd256_mask ((const __v4df *) __P,
(__v4df) __W,
(__mmask8) __U);
}
@@ -96,7 +96,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_load_pd (__mmask8 __U, void const *__P)
{
- return (__m256d) __builtin_ia32_loadapd256_mask ((__v4df *) __P,
+ return (__m256d) __builtin_ia32_loadapd256_mask ((const __v4df *) __P,
(__v4df)
_mm256_setzero_pd (),
(__mmask8) __U);
@@ -106,7 +106,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_load_pd (__m128d __W, __mmask8 __U, void const *__P)
{
- return (__m128d) __builtin_ia32_loadapd128_mask ((__v2df *) __P,
+ return (__m128d) __builtin_ia32_loadapd128_mask ((const __v2df *) __P,
(__v2df) __W,
(__mmask8) __U);
}
@@ -115,7 +115,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_load_pd (__mmask8 __U, void const *__P)
{
- return (__m128d) __builtin_ia32_loadapd128_mask ((__v2df *) __P,
+ return (__m128d) __builtin_ia32_loadapd128_mask ((const __v2df *) __P,
(__v2df)
_mm_setzero_pd (),
(__mmask8) __U);
@@ -181,7 +181,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_load_ps (__m256 __W, __mmask8 __U, void const *__P)
{
- return (__m256) __builtin_ia32_loadaps256_mask ((__v8sf *) __P,
+ return (__m256) __builtin_ia32_loadaps256_mask ((const __v8sf *) __P,
(__v8sf) __W,
(__mmask8) __U);
}
@@ -190,7 +190,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_load_ps (__mmask8 __U, void const *__P)
{
- return (__m256) __builtin_ia32_loadaps256_mask ((__v8sf *) __P,
+ return (__m256) __builtin_ia32_loadaps256_mask ((const __v8sf *) __P,
(__v8sf)
_mm256_setzero_ps (),
(__mmask8) __U);
@@ -200,7 +200,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_load_ps (__m128 __W, __mmask8 __U, void const *__P)
{
- return (__m128) __builtin_ia32_loadaps128_mask ((__v4sf *) __P,
+ return (__m128) __builtin_ia32_loadaps128_mask ((const __v4sf *) __P,
(__v4sf) __W,
(__mmask8) __U);
}
@@ -209,7 +209,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_load_ps (__mmask8 __U, void const *__P)
{
- return (__m128) __builtin_ia32_loadaps128_mask ((__v4sf *) __P,
+ return (__m128) __builtin_ia32_loadaps128_mask ((const __v4sf *) __P,
(__v4sf)
_mm_setzero_ps (),
(__mmask8) __U);
@@ -275,14 +275,14 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_load_epi64 (void const *__P)
{
- return (__m256i) (*(__v4di *) __P);
+ return (__m256i) (*(const __v4di *) __P);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_load_epi64 (__m256i __W, __mmask8 __U, void const *__P)
{
- return (__m256i) __builtin_ia32_movdqa64load256_mask ((__v4di *) __P,
+ return (__m256i) __builtin_ia32_movdqa64load256_mask ((const __v4di *) __P,
(__v4di) __W,
(__mmask8)
__U);
@@ -292,7 +292,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_load_epi64 (__mmask8 __U, void const *__P)
{
- return (__m256i) __builtin_ia32_movdqa64load256_mask ((__v4di *) __P,
+ return (__m256i) __builtin_ia32_movdqa64load256_mask ((const __v4di *) __P,
(__v4di)
_mm256_setzero_si256 (),
(__mmask8)
@@ -303,14 +303,14 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_load_epi64 (void const *__P)
{
- return (__m128i) (*(__v2di *) __P);
+ return (__m128i) (*(const __v2di *) __P);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_load_epi64 (__m128i __W, __mmask8 __U, void const *__P)
{
- return (__m128i) __builtin_ia32_movdqa64load128_mask ((__v2di *) __P,
+ return (__m128i) __builtin_ia32_movdqa64load128_mask ((const __v2di *) __P,
(__v2di) __W,
(__mmask8)
__U);
@@ -320,7 +320,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_load_epi64 (__mmask8 __U, void const *__P)
{
- return (__m128i) __builtin_ia32_movdqa64load128_mask ((__v2di *) __P,
+ return (__m128i) __builtin_ia32_movdqa64load128_mask ((const __v2di *) __P,
(__v2di)
_mm_setzero_si128 (),
(__mmask8)
@@ -387,14 +387,14 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_load_epi32 (void const *__P)
{
- return (__m256i) (*(__v8si *) __P);
+ return (__m256i) (*(const __v8si *) __P);
}
extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_load_epi32 (__m256i __W, __mmask8 __U, void const *__P)
{
- return (__m256i) __builtin_ia32_movdqa32load256_mask ((__v8si *) __P,
+ return (__m256i) __builtin_ia32_movdqa32load256_mask ((const __v8si *) __P,
(__v8si) __W,
(__mmask8)
__U);
@@ -404,7 +404,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_load_epi32 (__mmask8 __U, void const *__P)
{
- return (__m256i) __builtin_ia32_movdqa32load256_mask ((__v8si *) __P,
+ return (__m256i) __builtin_ia32_movdqa32load256_mask ((const __v8si *) __P,
(__v8si)
_mm256_setzero_si256 (),
(__mmask8)
@@ -415,14 +415,14 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_load_epi32 (void const *__P)
{
- return (__m128i) (*(__v4si *) __P);
+ return (__m128i) (*(const __v4si *) __P);
}
extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_load_epi32 (__m128i __W, __mmask8 __U, void const *__P)
{
- return (__m128i) __builtin_ia32_movdqa32load128_mask ((__v4si *) __P,
+ return (__m128i) __builtin_ia32_movdqa32load128_mask ((const __v4si *) __P,
(__v4si) __W,
(__mmask8)
__U);
@@ -432,7 +432,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_load_epi32 (__mmask8 __U, void const *__P)
{
- return (__m128i) __builtin_ia32_movdqa32load128_mask ((__v4si *) __P,
+ return (__m128i) __builtin_ia32_movdqa32load128_mask ((const __v4si *) __P,
(__v4si)
_mm_setzero_si128 (),
(__mmask8)
@@ -771,7 +771,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_loadu_epi64 (void const *__P)
{
- return (__m256i) (*(__v4di_u *) __P);
+ return (__m256i) (*(const __v4di_u *) __P);
}
extern __inline __m256i
@@ -797,7 +797,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_loadu_epi64 (void const *__P)
{
- return (__m128i) (*(__v2di_u *) __P);
+ return (__m128i) (*(const __v2di_u *) __P);
}
extern __inline __m128i
@@ -855,7 +855,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_loadu_epi32 (void const *__P)
{
- return (__m256i) (*(__v8si_u *) __P);
+ return (__m256i) (*(const __v8si_u *) __P);
}
extern __inline __m256i
@@ -881,7 +881,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_loadu_epi32 (void const *__P)
{
- return (__m128i) (*(__v4si_u *) __P);
+ return (__m128i) (*(const __v4si_u *) __P);
}
extern __inline __m128i
@@ -6130,7 +6130,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_expandloadu_pd (__m256d __W, __mmask8 __U, void const *__P)
{
- return (__m256d) __builtin_ia32_expandloaddf256_mask ((__v4df *) __P,
+ return (__m256d) __builtin_ia32_expandloaddf256_mask ((const __v4df *) __P,
(__v4df) __W,
(__mmask8)
__U);
@@ -6140,7 +6140,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_expandloadu_pd (__mmask8 __U, void const *__P)
{
- return (__m256d) __builtin_ia32_expandloaddf256_maskz ((__v4df *) __P,
+ return (__m256d) __builtin_ia32_expandloaddf256_maskz ((const __v4df *) __P,
(__v4df)
_mm256_setzero_pd (),
(__mmask8)
@@ -6170,7 +6170,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_expandloadu_pd (__m128d __W, __mmask8 __U, void const *__P)
{
- return (__m128d) __builtin_ia32_expandloaddf128_mask ((__v2df *) __P,
+ return (__m128d) __builtin_ia32_expandloaddf128_mask ((const __v2df *) __P,
(__v2df) __W,
(__mmask8)
__U);
@@ -6180,7 +6180,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_expandloadu_pd (__mmask8 __U, void const *__P)
{
- return (__m128d) __builtin_ia32_expandloaddf128_maskz ((__v2df *) __P,
+ return (__m128d) __builtin_ia32_expandloaddf128_maskz ((const __v2df *) __P,
(__v2df)
_mm_setzero_pd (),
(__mmask8)
@@ -6210,7 +6210,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_mask_expandloadu_ps (__m256 __W, __mmask8 __U, void const *__P)
{
- return (__m256) __builtin_ia32_expandloadsf256_mask ((__v8sf *) __P,
+ return (__m256) __builtin_ia32_expandloadsf256_mask ((const __v8sf *) __P,
(__v8sf) __W,
(__mmask8) __U);
}
@@ -6219,7 +6219,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_expandloadu_ps (__mmask8 __U, void const *__P)
{
- return (__m256) __builtin_ia32_expandloadsf256_maskz ((__v8sf *) __P,
+ return (__m256) __builtin_ia32_expandloadsf256_maskz ((const __v8sf *) __P,
(__v8sf)
_mm256_setzero_ps (),
(__mmask8)
@@ -6249,7 +6249,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_expandloadu_ps (__m128 __W, __mmask8 __U, void const *__P)
{
- return (__m128) __builtin_ia32_expandloadsf128_mask ((__v4sf *) __P,
+ return (__m128) __builtin_ia32_expandloadsf128_mask ((const __v4sf *) __P,
(__v4sf) __W,
(__mmask8) __U);
}
@@ -6258,7 +6258,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_expandloadu_ps (__mmask8 __U, void const *__P)
{
- return (__m128) __builtin_ia32_expandloadsf128_maskz ((__v4sf *) __P,
+ return (__m128) __builtin_ia32_expandloadsf128_maskz ((const __v4sf *) __P,
(__v4sf)
_mm_setzero_ps (),
(__mmask8)
@@ -6289,7 +6289,7 @@
_mm256_mask_expandloadu_epi64 (__m256i __W, __mmask8 __U,
void const *__P)
{
- return (__m256i) __builtin_ia32_expandloaddi256_mask ((__v4di *) __P,
+ return (__m256i) __builtin_ia32_expandloaddi256_mask ((const __v4di *) __P,
(__v4di) __W,
(__mmask8)
__U);
@@ -6299,7 +6299,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_expandloadu_epi64 (__mmask8 __U, void const *__P)
{
- return (__m256i) __builtin_ia32_expandloaddi256_maskz ((__v4di *) __P,
+ return (__m256i) __builtin_ia32_expandloaddi256_maskz ((const __v4di *) __P,
(__v4di)
_mm256_setzero_si256 (),
(__mmask8)
@@ -6329,7 +6329,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_expandloadu_epi64 (__m128i __W, __mmask8 __U, void const *__P)
{
- return (__m128i) __builtin_ia32_expandloaddi128_mask ((__v2di *) __P,
+ return (__m128i) __builtin_ia32_expandloaddi128_mask ((const __v2di *) __P,
(__v2di) __W,
(__mmask8)
__U);
@@ -6339,7 +6339,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_expandloadu_epi64 (__mmask8 __U, void const *__P)
{
- return (__m128i) __builtin_ia32_expandloaddi128_maskz ((__v2di *) __P,
+ return (__m128i) __builtin_ia32_expandloaddi128_maskz ((const __v2di *) __P,
(__v2di)
_mm_setzero_si128 (),
(__mmask8)
@@ -6370,7 +6370,7 @@
_mm256_mask_expandloadu_epi32 (__m256i __W, __mmask8 __U,
void const *__P)
{
- return (__m256i) __builtin_ia32_expandloadsi256_mask ((__v8si *) __P,
+ return (__m256i) __builtin_ia32_expandloadsi256_mask ((const __v8si *) __P,
(__v8si) __W,
(__mmask8)
__U);
@@ -6380,7 +6380,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_maskz_expandloadu_epi32 (__mmask8 __U, void const *__P)
{
- return (__m256i) __builtin_ia32_expandloadsi256_maskz ((__v8si *) __P,
+ return (__m256i) __builtin_ia32_expandloadsi256_maskz ((const __v8si *) __P,
(__v8si)
_mm256_setzero_si256 (),
(__mmask8)
@@ -6410,7 +6410,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_mask_expandloadu_epi32 (__m128i __W, __mmask8 __U, void const *__P)
{
- return (__m128i) __builtin_ia32_expandloadsi128_mask ((__v4si *) __P,
+ return (__m128i) __builtin_ia32_expandloadsi128_mask ((const __v4si *) __P,
(__v4si) __W,
(__mmask8)
__U);
@@ -6420,7 +6420,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_maskz_expandloadu_epi32 (__mmask8 __U, void const *__P)
{
- return (__m128i) __builtin_ia32_expandloadsi128_maskz ((__v4si *) __P,
+ return (__m128i) __builtin_ia32_expandloadsi128_maskz ((const __v4si *) __P,
(__v4si)
_mm_setzero_si128 (),
(__mmask8)
--- /usr/src/external/gpl3/gcc/dist/gcc/config/i386/avxintrin.h 2023-07-30 10:11:56.822854938 +0200
+++ /usr/src/external/gpl3/gcc/dist/gcc/config/i386/avxintrin.h.new 2025-02-22 11:07:03.892404760 +0100
@@ -866,7 +866,7 @@
extern __inline __m256d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
_mm256_load_pd (double const *__P)
{
- return *(__m256d *)__P;
+ return *(const __m256d *)__P;
}
extern __inline void __attribute__((__gnu_inline__, __always_inline__, __artificial__))
@@ -878,7 +878,7 @@
extern __inline __m256 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
_mm256_load_ps (float const *__P)
{
- return *(__m256 *)__P;
+ return *(const __m256 *)__P;
}
extern __inline void __attribute__((__gnu_inline__, __always_inline__, __artificial__))
@@ -890,7 +890,7 @@
extern __inline __m256d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
_mm256_loadu_pd (double const *__P)
{
- return *(__m256d_u *)__P;
+ return *(const __m256d_u *)__P;
}
extern __inline void __attribute__((__gnu_inline__, __always_inline__, __artificial__))
@@ -902,7 +902,7 @@
extern __inline __m256 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
_mm256_loadu_ps (float const *__P)
{
- return *(__m256_u *)__P;
+ return *(const __m256_u *)__P;
}
extern __inline void __attribute__((__gnu_inline__, __always_inline__, __artificial__))
--- /usr/src/external/gpl3/gcc/dist/gcc/config/i386/keylockerintrin.h 2023-07-30 07:21:03.000000000 +0200
+++ /usr/src/external/gpl3/gcc/dist/gcc/config/i386/keylockerintrin.h.new 2025-02-22 11:07:03.896372098 +0100
@@ -99,28 +99,28 @@
unsigned char __attribute__((__gnu_inline__, __always_inline__, __artificial__))
_mm_aesdecwide128kl_u8(__m128i __A[8], const __m128i __B[8], const void * __P)
{
- return __builtin_ia32_aesdecwide128kl_u8 ((__v2di *) __A, (__v2di *) __B, __P);
+ return __builtin_ia32_aesdecwide128kl_u8 ((__v2di *) __A, (const __v2di *) __B, __P);
}
extern __inline
unsigned char __attribute__((__gnu_inline__, __always_inline__, __artificial__))
_mm_aesdecwide256kl_u8(__m128i __A[8], const __m128i __B[8], const void * __P)
{
- return __builtin_ia32_aesdecwide256kl_u8 ((__v2di *) __A, (__v2di *) __B, __P);
+ return __builtin_ia32_aesdecwide256kl_u8 ((__v2di *) __A, (const __v2di *) __B, __P);
}
extern __inline
unsigned char __attribute__((__gnu_inline__, __always_inline__, __artificial__))
_mm_aesencwide128kl_u8(__m128i __A[8], const __m128i __B[8], const void * __P)
{
- return __builtin_ia32_aesencwide128kl_u8 ((__v2di *) __A, (__v2di *) __B, __P);
+ return __builtin_ia32_aesencwide128kl_u8 ((__v2di *) __A, (const __v2di *) __B, __P);
}
extern __inline
unsigned char __attribute__((__gnu_inline__, __always_inline__, __artificial__))
_mm_aesencwide256kl_u8(__m128i __A[8], const __m128i __B[8], const void * __P)
{
- return __builtin_ia32_aesencwide256kl_u8 ((__v2di *) __A, (__v2di *) __B, __P);
+ return __builtin_ia32_aesencwide256kl_u8 ((__v2di *) __A, (const __v2di *) __B, __P);
}
#ifdef __DISABLE_WIDEKL__
#undef __DISABLE_WIDEKL__
>Release-Note:
>Audit-Trail:
From: Onno van der Linden <o.vd.linden@quicknet.nl>
To: gnats-bugs@netbsd.org
Cc:
Subject: Re: bin/59093: compile errors for userland on amd64 with gcc and
-march=nativ
Date: Sat, 22 Feb 2025 15:40:40 +0100
It looks like nadj needs to be initialized to zero in lgammal_r() in
ld128/e_lgammal_r.c too (just like in __ieee754_lgamma_r() and
__ieee754_lgammaf_r()):
--- /usr/src/lib/libm/ld128/e_lgammal_r.c 2024-01-21 19:53:15.000000000 +0100
+++ /usr/src/lib/libm/ld128/e_lgammal_r.c.new 2025-02-22 15:35:03.976922498 +0100
@@ -221,7 +221,7 @@
long double
lgammal_r(long double x, int *signgamp)
{
- long double nadj,p,p1,p2,q,r,t,w,y,z;
+ long double nadj = 0,p,p1,p2,q,r,t,w,y,z;
uint64_t llx,lx;
int i;
uint16_t hx,ix;
From: "Christos Zoulas" <christos@netbsd.org>
To: gnats-bugs@gnats.NetBSD.org
Cc:
Subject: PR/59093 CVS commit: src/external/gpl3/gcc/dist/gcc/config/i386
Date: Sat, 22 Feb 2025 14:06:52 -0500
Module Name: src
Committed By: christos
Date: Sat Feb 22 19:06:51 UTC 2025
Modified Files:
src/external/gpl3/gcc/dist/gcc/config/i386: avx512bwintrin.h
avx512fintrin.h avx512vlbwintrin.h avx512vlintrin.h avxintrin.h
keylockerintrin.h
Log Message:
PR/59093: Onno van der Linden: Fix const casting warnings
To generate a diff of this commit:
cvs rdiff -u -r1.1.1.10 -r1.2 \
src/external/gpl3/gcc/dist/gcc/config/i386/avx512bwintrin.h \
src/external/gpl3/gcc/dist/gcc/config/i386/avx512vlbwintrin.h \
src/external/gpl3/gcc/dist/gcc/config/i386/avx512vlintrin.h
cvs rdiff -u -r1.1.1.12 -r1.2 \
src/external/gpl3/gcc/dist/gcc/config/i386/avx512fintrin.h
cvs rdiff -u -r1.1.1.13 -r1.2 \
src/external/gpl3/gcc/dist/gcc/config/i386/avxintrin.h
cvs rdiff -u -r1.1.1.1 -r1.2 \
src/external/gpl3/gcc/dist/gcc/config/i386/keylockerintrin.h
Please note that diffs are not public domain; they are subject to the
copyright notices on the relevant files.
From: "Christos Zoulas" <christos@netbsd.org>
To: gnats-bugs@gnats.NetBSD.org
Cc:
Subject: PR/59093 CVS commit: src/lib/libm/ld80
Date: Sat, 22 Feb 2025 14:09:05 -0500
Module Name: src
Committed By: christos
Date: Sat Feb 22 19:09:05 UTC 2025
Modified Files:
src/lib/libm/ld80: e_lgammal_r.c
Log Message:
PR/59093: Onno van der Linden: Elide compiler warning
To generate a diff of this commit:
cvs rdiff -u -r1.2 -r1.3 src/lib/libm/ld80/e_lgammal_r.c
Please note that diffs are not public domain; they are subject to the
copyright notices on the relevant files.
From: Onno van der Linden <o.vd.linden@quicknet.nl>
To: gnats-bugs@netbsd.org
Cc: christos@netbsd.org
Subject: Re: PR/59093 CVS commit: src/external/gpl3/gcc/dist/gcc/config/i386
Date: Sun, 23 Feb 2025 11:20:21 +0100
On Sat, Feb 22, 2025 at 07:10:02PM +0000, Christos Zoulas wrote:
> The following reply was made to PR bin/59093; it has been noted by GNATS.
>
> From: "Christos Zoulas" <christos@netbsd.org>
> To: gnats-bugs@gnats.NetBSD.org
> Cc:
> Subject: PR/59093 CVS commit: src/external/gpl3/gcc/dist/gcc/config/i386
> Date: Sat, 22 Feb 2025 14:06:52 -0500
>
> Module Name: src
> Committed By: christos
> Date: Sat Feb 22 19:06:51 UTC 2025
>
> Modified Files:
> src/external/gpl3/gcc/dist/gcc/config/i386: avx512bwintrin.h
> avx512fintrin.h avx512vlbwintrin.h avx512vlintrin.h avxintrin.h
> keylockerintrin.h
>
> Log Message:
> PR/59093: Onno van der Linden: Fix const casting warnings
This commit seems to be missing a fix for _mm256_stream_load_si256 in
avx2intrin.h. Instead of the #pragma GCC diagnostic ignored "-Wcast-qual"
fix I proposed earlier this type cast alternative might be "better":
--- avx2intrin.h.orig 2024-06-17 10:45:06.000000000 +0200
+++ avx2intrin.h 2025-02-23 04:56:13.677881010 +0100
@@ -919,7 +919,7 @@
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_stream_load_si256 (__m256i const *__X)
{
- return (__m256i) __builtin_ia32_movntdqa256 ((__v4di *) __X);
+ return (__m256i) __builtin_ia32_movntdqa256 ((__v4di *) (unsigned long)__X);
}
extern __inline __m128
From: Onno van der Linden <o.vd.linden@quicknet.nl>
To: gnats-bugs@netbsd.org
Cc: christos@netbsd.org
Subject: Re: PR/59093 CVS commit: src/lib/libm/ld80
Date: Sun, 23 Feb 2025 11:24:14 +0100
On Sat, Feb 22, 2025 at 07:10:04PM +0000, Christos Zoulas wrote:
> The following reply was made to PR bin/59093; it has been noted by GNATS.
>
> From: "Christos Zoulas" <christos@netbsd.org>
> To: gnats-bugs@gnats.NetBSD.org
> Cc:
> Subject: PR/59093 CVS commit: src/lib/libm/ld80
> Date: Sat, 22 Feb 2025 14:09:05 -0500
>
> Module Name: src
> Committed By: christos
> Date: Sat Feb 22 19:09:05 UTC 2025
>
> Modified Files:
> src/lib/libm/ld80: e_lgammal_r.c
>
> Log Message:
> PR/59093: Onno van der Linden: Elide compiler warning
>
I think the ld128/e_lgammal_r.c nadj=0 fix needs to be done too ?
--- src/lib/libm/ld128/e_lgammal_r.c 2024-01-21 19:53:15.000000000 +0100
+++ src/lib/libm/ld128/e_lgammal_r.c.new 2025-02-22 15:35:03.976922498 +0100
@@ -221,7 +221,7 @@
long double
lgammal_r(long double x, int *signgamp)
{
- long double nadj,p,p1,p2,q,r,t,w,y,z;
+ long double nadj = 0,p,p1,p2,q,r,t,w,y,z;
uint64_t llx,lx;
int i;
uint16_t hx,i
Onno
From: "Christos Zoulas" <christos@netbsd.org>
To: gnats-bugs@gnats.NetBSD.org
Cc:
Subject: PR/59093 CVS commit: src/external/gpl3/gcc/dist/gcc/config/i386
Date: Sun, 23 Feb 2025 10:33:49 -0500
Module Name: src
Committed By: christos
Date: Sun Feb 23 15:33:49 UTC 2025
Modified Files:
src/external/gpl3/gcc/dist/gcc/config/i386: avx2intrin.h
Log Message:
Pr/59093: Onno van der Linden: Elide cast-qual gcc warning
To generate a diff of this commit:
cvs rdiff -u -r1.1.1.13 -r1.2 \
src/external/gpl3/gcc/dist/gcc/config/i386/avx2intrin.h
Please note that diffs are not public domain; they are subject to the
copyright notices on the relevant files.
From: Christos Zoulas <christos@zoulas.com>
To: Onno van der Linden <o.vd.linden@quicknet.nl>
Cc: gnats-bugs@netbsd.org,
christos@netbsd.org
Subject: Re: PR/59093 CVS commit: src/external/gpl3/gcc/dist/gcc/config/i386
Date: Sun, 23 Feb 2025 10:34:08 -0500
--Apple-Mail=_15AFC5F6-076B-4185-8246-2AE5D891B960
Content-Transfer-Encoding: 7bit
Content-Type: text/plain;
charset=us-ascii
Committed, thanks!
christos
--Apple-Mail=_15AFC5F6-076B-4185-8246-2AE5D891B960
Content-Transfer-Encoding: 7bit
Content-Disposition: attachment;
filename=signature.asc
Content-Type: application/pgp-signature;
name=signature.asc
Content-Description: Message signed with OpenPGP
-----BEGIN PGP SIGNATURE-----
Comment: GPGTools - http://gpgtools.org
iF0EARECAB0WIQS+BJlbqPkO0MDBdsRxESqxbLM7OgUCZ7s/8AAKCRBxESqxbLM7
OqiDAJ0aS5H5M/7u0az1eEchzwoFf5pctACgyooxrd42am7ckG5GiV+TQMEzl3E=
=vbNT
-----END PGP SIGNATURE-----
--Apple-Mail=_15AFC5F6-076B-4185-8246-2AE5D891B960--
From: "Christos Zoulas" <christos@netbsd.org>
To: gnats-bugs@gnats.NetBSD.org
Cc:
Subject: PR/59093 CVS commit: src/lib/libm/ld128
Date: Sun, 23 Feb 2025 10:36:07 -0500
Module Name: src
Committed By: christos
Date: Sun Feb 23 15:36:07 UTC 2025
Modified Files:
src/lib/libm/ld128: e_lgammal_r.c
Log Message:
PR/59093: Onno van der Linden: Follow suit and do the same as the ld80 version
To generate a diff of this commit:
cvs rdiff -u -r1.1 -r1.2 src/lib/libm/ld128/e_lgammal_r.c
Please note that diffs are not public domain; they are subject to the
copyright notices on the relevant files.
From: Christos Zoulas <christos@zoulas.com>
To: Onno van der Linden <o.vd.linden@quicknet.nl>
Cc: gnats-bugs@netbsd.org,
christos@netbsd.org
Subject: Re: PR/59093 CVS commit: src/lib/libm/ld80
Date: Sun, 23 Feb 2025 10:36:20 -0500
--Apple-Mail=_E9FCAB1F-BD70-4E74-8997-913E0B3611AA
Content-Transfer-Encoding: 7bit
Content-Type: text/plain;
charset=us-ascii
You got it.
christos
--Apple-Mail=_E9FCAB1F-BD70-4E74-8997-913E0B3611AA
Content-Transfer-Encoding: 7bit
Content-Disposition: attachment;
filename=signature.asc
Content-Type: application/pgp-signature;
name=signature.asc
Content-Description: Message signed with OpenPGP
-----BEGIN PGP SIGNATURE-----
Comment: GPGTools - http://gpgtools.org
iF0EARECAB0WIQS+BJlbqPkO0MDBdsRxESqxbLM7OgUCZ7tAdAAKCRBxESqxbLM7
Ogx0AKCALCw3Rei+BLKac0NoDC2QHO3EeACeO65vcMQdK+5ICiqNMYg8HA1duEY=
=Ei3w
-----END PGP SIGNATURE-----
--Apple-Mail=_E9FCAB1F-BD70-4E74-8997-913E0B3611AA--
State-Changed-From-To: open->feedback
State-Changed-By: dholland@NetBSD.org
State-Changed-When: Tue, 25 Feb 2025 05:34:38 +0000
State-Changed-Why:
is this done, or do we want pullup-10, or are there still bits left?
From: Onno van der Linden <o.vd.linden@quicknet.nl>
To: gnats-bugs@netbsd.org
Cc:
Subject: Re: bin/59093 (Subject: compile errors for userland on amd64 with
gcc and -march=native)
Date: Tue, 25 Feb 2025 18:24:46 +0100
On Tue, Feb 25, 2025 at 05:34:38AM +0000, dholland@NetBSD.org wrote:
> Synopsis: Subject: compile errors for userland on amd64 with gcc and -march=native
>
> State-Changed-From-To: open->feedback
> State-Changed-By: dholland@NetBSD.org
> State-Changed-When: Tue, 25 Feb 2025 05:34:38 +0000
> State-Changed-Why:
> is this done, or do we want pullup-10, or are there still bits left?
Both my test cases (libm and zstd) compile and work fine with or without
-march=native. Looks like this can be closed.
Thanks very much,
Onno
From: Taylor R Campbell <riastradh@NetBSD.org>
To: Onno van der Linden <o.vd.linden@quicknet.nl>
Cc: gnats-bugs@NetBSD.org, netbsd-bugs@NetBSD.org,
christos@NetBSD.org, mrg@NetBSD.org
Subject: Re: bin/59093: compile errors for userland on amd64 with gcc and -march=native
Date: Wed, 26 Feb 2025 13:40:03 +0000
I don't understand, why are any changes to the gcc *intrin.h files
needed at all? Shouldn't the warnings be suppressed under the default
of -Wno-system-headers, unless you go out of your way to enable
-Wsystem-headers?
Initializing nadj in lgammal_r is harmless but we should mark it with
/* XXX gcc-12.whatever -march=native, PR bin/59093 */
because the variable is not actually used uninitialized -- the
initialization and the use are both conditional on `if (hx & 0x8000)'
(and only on that).
From: Christos Zoulas <christos@zoulas.com>
To: gnats-bugs@netbsd.org
Cc: gnats-admin@netbsd.org,
netbsd-bugs@netbsd.org,
Onno van der Linden <o.vd.linden@quicknet.nl>,
"riastradh@netbsd.org" <riastradh@NetBSD.org>,
"mrg@netbsd.org" <mrg@NetBSD.org>,
"christos@netbsd.org" <christos@NetBSD.org>
Subject: Re: bin/59093: compile errors for userland on amd64 with gcc and
-march=native
Date: Fri, 28 Feb 2025 11:04:44 -0500
--Apple-Mail=_15F760AC-F51C-44BB-AB4E-B6C4D127974D
Content-Transfer-Encoding: 7bit
Content-Type: text/plain;
charset=us-ascii
Yes, it is marked // XXX: gcc
christos
--Apple-Mail=_15F760AC-F51C-44BB-AB4E-B6C4D127974D
Content-Transfer-Encoding: 7bit
Content-Disposition: attachment;
filename=signature.asc
Content-Type: application/pgp-signature;
name=signature.asc
Content-Description: Message signed with OpenPGP
-----BEGIN PGP SIGNATURE-----
Comment: GPGTools - http://gpgtools.org
iF0EARECAB0WIQS+BJlbqPkO0MDBdsRxESqxbLM7OgUCZ8HenAAKCRBxESqxbLM7
OuNDAJ4owgUVUclzDflwKGMzNocseaSuAgCZAYC5gfFeJhKWVWvSVLR7ONvd4mU=
=ZwSU
-----END PGP SIGNATURE-----
--Apple-Mail=_15F760AC-F51C-44BB-AB4E-B6C4D127974D--
>Unformatted:
(Contact us)
$NetBSD: query-full-pr,v 1.47 2022/09/11 19:34:41 kim Exp $
$NetBSD: gnats_config.sh,v 1.9 2014/08/02 14:16:04 spz Exp $
Copyright © 1994-2025
The NetBSD Foundation, Inc. ALL RIGHTS RESERVED.
Home