public inbox for passt-dev@passt.top
 help / color / mirror / code / Atom feed
From: Stefano Brivio <sbrivio@redhat.com>
To: David Gibson <david@gibson.dropbear.id.au>
Cc: Yumei Huang <yuhuang@redhat.com>, passt-dev@passt.top
Subject: Re: [PATCH v3 2/4] util: Introduce read_file() and read_file_long() function
Date: Wed, 29 Oct 2025 17:23:13 +0100	[thread overview]
Message-ID: <20251029172313.2e7b51e0@elisabeth> (raw)
In-Reply-To: <aQHfzAlgeqapGZuo@zatzit>

On Wed, 29 Oct 2025 20:35:08 +1100
David Gibson <david@gibson.dropbear.id.au> wrote:

> On Wed, Oct 29, 2025 at 05:43:16AM +0100, Stefano Brivio wrote:
> > On Wed, 29 Oct 2025 11:43:00 +1100
> > David Gibson <david@gibson.dropbear.id.au> wrote:
> >   
> > > On Wed, Oct 29, 2025 at 12:12:48AM +0100, Stefano Brivio wrote:  
> [snip]
> > > > By the way, while it doesn't cover intmax_t explicitly, I think this is
> > > > a pretty good resource as it covers most architectures supported by the
> > > > Linux kernel (hence, most architectures we support):
> > > > 
> > > >   https://wiki.debian.org/ArchitectureSpecificsMemo#Summary    
> > > 
> > > Oh, nice, that is a very handy resource.
> > >   
> > > > and judging from intmax_t(3type) I'd say that the sizeof(long double)
> > > > column tells you how big intmax_t is.    
> > >   
> > > > Well, at least, that's the page I use to know which architectures I can
> > > > use to check things when I suspect a type portability bug.
> > > > 
> > > > That's because 'long double' should always be the biggest "native" data
> > > > type, that is, excluding __int128 or vectorised / SIMD types such as
> > > > __m256i.    
> > > 
> > > This part isn't true, alas.  Theoretically speaking there's not
> > > necessarily any relation between the largest native integer type and
> > > the largest native float type.  
> > 
> > Oops, yes, I misread intmax_t(3type), that's *integer* only (of course,
> > the name says it). So probably it has to match sizeof(long long)?
> >   
> > > But more importantly, it's not true in practice: according to the
> > > table sizeof(long double) is 16 for amd64, but sizeof(intmax_t) is 8
> > > empirically.
> > > 
> > > I think sizeof(long long) is more likely to match sizeof(intmax_t),
> > > but I don't love relying on it.  
> > 
> > Right... well, about relying on it, without a change in the C11
> > standard, can it ever differ? I don't think so. We could have a look at
> > C17 / C23 and if long long is still the largest integer type, we know
> > we're fine for quite a few years / pretty much forever.  
> 
> Uh.. maybe?  I'm never clear on what's guaranteed by the C standard
> and what's left to the platform / ABI.  AIUI the reason for intmax_t's
> existence is because an awful lot is not pinned down by the standard.

The standard specifies long long, without a width, and not long long
long, so we know that long long is the longest we can have at the
moment.

> __int128 does appear to be a thing that is longer than long long.

Yes but that's what I meant by "native" type, for lack of a better
name. It looks like they're more commonly called "main" types instead.

__int128 is a GNU extension and specifies a 128-bit width just like
__m256i specifies a 256-bit width. Those can be bigger than intmax_t.

> Maybe there's a rule that doesn't allow intmax_t to be __int128, but
> I'm not sure where we'd find it.

No real rule but BUGS in intmax_t(3type) reports this (even though it
doesn't look like a bug to me).

-- 
Stefano


  reply	other threads:[~2025-10-29 16:23 UTC|newest]

Thread overview: 31+ messages / expand[flat|nested]  mbox.gz  Atom feed  top
2025-10-14  7:38 [PATCH v3 0/4] Retry SYNs for inbound connections Yumei Huang
2025-10-14  7:38 ` [PATCH v3 1/4] tcp: Rename "retrans" to "retries" Yumei Huang
2025-10-14 22:50   ` David Gibson
2025-10-15  2:17     ` Yumei Huang
2025-10-14  7:38 ` [PATCH v3 2/4] util: Introduce read_file() and read_file_long() function Yumei Huang
2025-10-14 23:27   ` David Gibson
2025-10-15  3:50     ` Yumei Huang
2025-10-15  4:46       ` David Gibson
2025-10-15  5:46         ` Yumei Huang
2025-10-28 23:12         ` Stefano Brivio
2025-10-29  0:43           ` David Gibson
2025-10-29  4:43             ` Stefano Brivio
2025-10-29  9:35               ` David Gibson
2025-10-29 16:23                 ` Stefano Brivio [this message]
2025-10-14  7:38 ` [PATCH v3 3/4] tcp: Resend SYN for inbound connections Yumei Huang
2025-10-14 23:40   ` David Gibson
2025-10-14  7:38 ` [PATCH v3 4/4] tcp: Update data retransmission timeout Yumei Huang
2025-10-15  0:05   ` David Gibson
2025-10-15  6:31     ` Yumei Huang
2025-10-15 22:54       ` David Gibson
2025-10-17 18:28         ` Stefano Brivio
2025-10-20  0:20           ` David Gibson
2025-10-20  5:11             ` Stefano Brivio
2025-10-20  9:17               ` David Gibson
2025-10-28 23:13                 ` Stefano Brivio
2025-10-29  0:35                   ` David Gibson
2025-10-29  4:52                     ` Stefano Brivio
2025-10-29  9:37                       ` David Gibson
2025-10-20 10:57           ` Yumei Huang
2025-10-20 23:20             ` Stefano Brivio
2025-10-22  2:23               ` David Gibson

Reply instructions:

You may reply publicly to this message via plain-text email
using any one of the following methods:

* Save the following mbox file, import it into your mail client,
  and reply-to-all from there: mbox

  Avoid top-posting and favor interleaved quoting:
  https://en.wikipedia.org/wiki/Posting_style#Interleaved_style

* Reply using the --to, --cc, and --in-reply-to
  switches of git-send-email(1):

  git send-email \
    --in-reply-to=20251029172313.2e7b51e0@elisabeth \
    --to=sbrivio@redhat.com \
    --cc=david@gibson.dropbear.id.au \
    --cc=passt-dev@passt.top \
    --cc=yuhuang@redhat.com \
    /path/to/YOUR_REPLY

  https://kernel.org/pub/software/scm/git/docs/git-send-email.html

* If your mail client supports setting the In-Reply-To header
  via mailto: links, try the mailto: link
Be sure your reply has a Subject: header at the top and a blank line before the message body.
Code repositories for project(s) associated with this public inbox

	https://passt.top/passt

This is a public inbox, see mirroring instructions
for how to clone and mirror all data and code used for this inbox;
as well as URLs for IMAP folder(s).