IA32 System V Application Binary Interface

Contact owners and managers

1–30 of 32

This is the place to discuss modification and extension of IA32 processor specific System V Application Binary Interface. The current ia32 psABI source is on hjl/x86/master branch at

https://github.com/hjl-tools/x86-psABI/tree/hjl/x86/master

0 selected

H.J. Lu, … John McCall14

8/25/21

[PATCH] Add optional _Float16 support

On Wed, Aug 25, 2021 at 8:36 AM HJ Lu <hjl....@gmail.com> wrote: On Mon, Aug 23, 2021 at 10:

unread,

[PATCH] Add optional _Float16 support

On Wed, Aug 25, 2021 at 8:36 AM HJ Lu <hjl....@gmail.com> wrote: On Mon, Aug 23, 2021 at 10:

8/25/21

Thiago Macieira, H.J. Lu2

5/3/20

Passing constrained enums via ...: should they be zero-extended to register size?

On Thu, Apr 30, 2020 at 7:56 PM Thiago Macieira <thi...@macieira.org> wrote: > > Code:

unread,

Passing constrained enums via ...: should they be zero-extended to register size?

On Thu, Apr 30, 2020 at 7:56 PM Thiago Macieira <thi...@macieira.org> wrote: > > Code:

5/3/20

4/2/20

How to determine the alignment arguments on the stack of struct or union for argument passing?

The gcc version I use is 7.3.0 and the option is -m32. For example: #include <immintrin.h>

unread,

How to determine the alignment arguments on the stack of struct or union for argument passing?

The gcc version I use is 7.3.0 and the option is -m32. For example: #include <immintrin.h>

4/2/20

Jonathan Wakely, … John McCall23

9/11/19

Alignment requirements for _Atomic should be stated

On Wednesday, March 20, 2019 at 4:44:30 PM UTC-4, Jonathan Wakely wrote: On Wednesday, 2 January 2019

unread,

Alignment requirements for _Atomic should be stated

On Wednesday, March 20, 2019 at 4:44:30 PM UTC-4, Jonathan Wakely wrote: On Wednesday, 2 January 2019

9/11/19

2/21/19

RFC: Update x86 psABIs to support IBT

On Thu, Feb 21, 2019 at 2:30 PM Rui Ueyama <ru...@google.com> wrote: > > On Thu, Feb 21,

unread,

RFC: Update x86 psABIs to support IBT

On Thu, Feb 21, 2019 at 2:30 PM Rui Ueyama <ru...@google.com> wrote: > > On Thu, Feb 21,

2/21/19

12/22/18

The Intel386 psABI draft updated with program property is available

It includes Intel Control-flow Enforcement Technology (CET) support: https://github.com/hjl-tools/x86

unread,

The Intel386 psABI draft updated with program property is available

It includes Intel Control-flow Enforcement Technology (CET) support: https://github.com/hjl-tools/x86

12/22/18

5/29/18

Parameters store on stack is preserved across function call or volatile in ABI of intel386 & amd64?

Hi Is the parameters stored on the stack preserved across function calls or volatile in the ABI of

unread,

Parameters store on stack is preserved across function call or volatile in ABI of intel386 & amd64?

Hi Is the parameters stored on the stack preserved across function calls or volatile in the ABI of

5/29/18

9/6/17

Description of _Bool in registers (outside of arg-passing / returning) is overly specific.

Section 2.1.1 includes this language: Booleans, when stored in a memory object, are stored as single

unread,

Description of _Bool in registers (outside of arg-passing / returning) is overly specific.

Section 2.1.1 includes this language: Booleans, when stored in a memory object, are stored as single

9/6/17

H.J. Lu, … Michael Matz13

8/7/17

RFC: Add R_X86_64_GPOFF/R_386_GPOFF relocation

Hi, On Mon, 7 Aug 2017, HJ Lu wrote: > > Before removing the last segment register from general

unread,

RFC: Add R_X86_64_GPOFF/R_386_GPOFF relocation

Hi, On Mon, 7 Aug 2017, HJ Lu wrote: > > Before removing the last segment register from general

8/7/17

H.J. Lu, … Florian Weimer9

7/28/17

RFC: Update x86 psABI to support shadow stac

On Fri, Jul 28, 2017 at 7:59 AM, Florian Weimer <fwe...@redhat.com> wrote: > On 07/27/2017

unread,

RFC: Update x86 psABI to support shadow stac

On Fri, Jul 28, 2017 at 7:59 AM, Florian Weimer <fwe...@redhat.com> wrote: > On 07/27/2017

7/28/17

6/14/17

RFC: Update i386 psABI to support ENDBR

On Tue, Jun 13, 2017 at 12:11 PM, HJ Lu <hjl....@gmail.com> wrote: > To support ENDBR in

unread,

RFC: Update i386 psABI to support ENDBR

On Tue, Jun 13, 2017 at 12:11 PM, HJ Lu <hjl....@gmail.com> wrote: > To support ENDBR in

6/14/17

H.J. Lu, Rafael Espíndola4

4/3/17

Clarify R_386_GOT32 and R_386_GOT32X relocations

On Thu, Mar 30, 2017 at 12:50 PM, Rafael Espíndola <rafael.e...@gmail.com> wrote: > On

unread,

Clarify R_386_GOT32 and R_386_GOT32X relocations

On Thu, Mar 30, 2017 at 12:50 PM, Rafael Espíndola <rafael.e...@gmail.com> wrote: > On

4/3/17

6/24/16

RFC: Call external functions without PLT

Procedure Linkage Table (PLT) is used to access external functions defined in shared object and

unread,

RFC: Call external functions without PLT

Procedure Linkage Table (PLT) is used to access external functions defined in shared object and

6/24/16

4/24/16

Convert load via GOT slot to load immediate

We should covert mov foo@GOT, %reg2 and mov foo@GOT(%reg1), %reg2 to mov $foo, %reg2 instead of lea

unread,

Convert load via GOT slot to load immediate

We should covert mov foo@GOT, %reg2 and mov foo@GOT(%reg1), %reg2 to mov $foo, %reg2 instead of lea

4/24/16

H.J. Lu, Thiago Macieira4

12/7/15

RFC: Intel386 psABI version 1.1 draft

On Tue, Nov 24, 2015 at 8:16 AM, HJ Lu <hjl....@gmail.com> wrote: > Hi, > > Here is

unread,

RFC: Intel386 psABI version 1.1 draft

On Tue, Nov 24, 2015 at 8:16 AM, HJ Lu <hjl....@gmail.com> wrote: > Hi, > > Here is

12/7/15

10/20/15

RCF: Add R_386_GOT32X

On Thu, Oct 15, 2015 at 8:54 AM, HJ Lu <hjl....@gmail.com> wrote: > X86 instruction

unread,

RCF: Add R_386_GOT32X

On Thu, Oct 15, 2015 at 8:54 AM, HJ Lu <hjl....@gmail.com> wrote: > X86 instruction

10/20/15

Rafael Espíndola, … H.J. Lu7

9/30/15

What exactly does R_386_PC32 point to?

>> Hope that helps (and I didn't mess up details too much), >> Alexander I does,

unread,

What exactly does R_386_PC32 point to?

>> Hope that helps (and I didn't mess up details too much), >> Alexander I does,

9/30/15

7/3/15

RFC: A new psABI for Intel MCU

On Mon, May 11, 2015 at 6:43 AM, HJ Lu <hjl....@gmail.com> wrote: > I am working on a new

unread,

RFC: A new psABI for Intel MCU

On Mon, May 11, 2015 at 6:43 AM, HJ Lu <hjl....@gmail.com> wrote: > I am working on a new

7/3/15

5/29/15

Re: Relocations to use when eliding plts

On Fri, May 29, 2015 at 10:59 AM, HJ Lu <hjl....@gmail.com> wrote: > On Fri, May 29, 2015

unread,

Re: Relocations to use when eliding plts

On Fri, May 29, 2015 at 10:59 AM, HJ Lu <hjl....@gmail.com> wrote: > On Fri, May 29, 2015

5/29/15

5/18/15

RFC: Add a new relocation to x86-64/i386 psABIs

On Mon, May 18, 2015 at 8:52 AM, Michael Matz <ma...@suse.de> wrote: > Hi, > > On Mon,

unread,

RFC: Add a new relocation to x86-64/i386 psABIs

On Mon, May 18, 2015 at 8:52 AM, Michael Matz <ma...@suse.de> wrote: > Hi, > > On Mon,

5/18/15

2/19/15

RFC: Update Intel386 psABI for AVX-512

Hi, I updated Intel386 psABI for AVX-512. It is on hjl/x86/avx512 branch at https://github.com/hjl-

unread,

RFC: Update Intel386 psABI for AVX-512

Hi, I updated Intel386 psABI for AVX-512. It is on hjl/x86/avx512 branch at https://github.com/hjl-

2/19/15

H.J. Lu, Michael Eager4

2/19/15

ANNOUNCEMENT: Intel386 psABI version 1.0

On Mon, Feb 16, 2015 at 9:54 AM, HJ Lu <hjl....@gmail.com> wrote: > On Fri, Feb 6, 2015 at

unread,

ANNOUNCEMENT: Intel386 psABI version 1.0

On Mon, Feb 16, 2015 at 9:54 AM, HJ Lu <hjl....@gmail.com> wrote: > On Fri, Feb 6, 2015 at

2/19/15

H.J. Lu, Joseph Myers3

1/22/15

RFC: IA-32 psABI draft version 0.1

On Thu, Jan 22, 2015 at 6:33 AM, Joseph Myers <jos...@codesourcery.com> wrote: > I would

unread,

RFC: IA-32 psABI draft version 0.1

On Thu, Jan 22, 2015 at 6:33 AM, Joseph Myers <jos...@codesourcery.com> wrote: > I would

1/22/15

11/7/14

Require REX prefix to encode R_X86_64_GOTTPOFF

Please ignore this. I should posit it to x32 psABI group. On Friday, November 7, 2014 12:42:59 PM UTC

unread,

Require REX prefix to encode R_X86_64_GOTTPOFF

Please ignore this. I should posit it to x32 psABI group. On Friday, November 7, 2014 12:42:59 PM UTC

11/7/14

11/19/13

x86-64 psABI group

Hi, I created: https://groups.google.com/forum/?hl=en#!forum/x86-64-abi to cover x86-64 psABI. Anyone

unread,

x86-64 psABI group

Hi, I created: https://groups.google.com/forum/?hl=en#!forum/x86-64-abi to cover x86-64 psABI. Anyone

11/19/13

10/9/13

X86-64 System V Application Binary Interface group announcement

Hi, www.x86-64.org was down for several months and it is up now, but not in its full capacity. I

unread,

X86-64 System V Application Binary Interface group announcement

Hi, www.x86-64.org was down for several months and it is up now, but not in its full capacity. I

10/9/13

peter, Michael Eager2

12/16/09

peter wrote: > Hi all, where I can find a simple ELF loader that compatible with > (System V

unread,

peter wrote: > Hi all, where I can find a simple ELF loader that compatible with > (System V

12/16/09

H.J. Lu, … Ian Lance Taylor23

6/8/09

Proposal for STT_GNU_IFUNC and R_*_IRELATIVE

On Mon, Jun 8, 2009 at 6:30 AM, Paul Brook<pa...@codesourcery.com> wrote: >> The only

unread,

Proposal for STT_GNU_IFUNC and R_*_IRELATIVE

On Mon, Jun 8, 2009 at 6:30 AM, Paul Brook<pa...@codesourcery.com> wrote: >> The only

6/8/09

H.J., … Dave Kreitzer7

4/1/08

How should _Decimal64 and _Decimal128 be aligned on stack?

Hi David, I added gcc mailing list. HJ On Tue, Apr 1, 2008 at 10:53 AM, Dave Kreitzer <david.l.

unread,

How should _Decimal64 and _Decimal128 be aligned on stack?

Hi David, I added gcc mailing list. HJ On Tue, Apr 1, 2008 at 10:53 AM, Dave Kreitzer <david.l.

4/1/08

hon...@gmail.com, … Mats Wichmann10

8/23/07

IA32/X86-64 TLS extensions

HJ Lu wrote: > On Wed, Aug 22, 2007 at 06:01:49PM -0300, Alexandre Oliva wrote: > >> Are

unread,

IA32/X86-64 TLS extensions

HJ Lu wrote: > On Wed, Aug 22, 2007 at 06:01:49PM -0300, Alexandre Oliva wrote: > >> Are

8/23/07

Search

Clear search

Close search

Google apps

Main menu