U
Который _start или который main?
Тогда ответь на это
Size: a a a
2020 March 16
U
Если прям в самом-самом энтрипоинте, то там нет адреса возврата на большинстве платформ
U
походу это под переменные argc и argv ...
Они как раз занимают с выравниванием 16 байт
U
Поэтому на него не влияют
U
На стеке минимальное выравнивание на x86/арме/ещё чем - sizeof(void*)
U
Однако calling convention'ы почему то требуют 16 байт на фрейм
ЕК
утверджается что после вычитания 8 из начального значения esp он станет кратным 16ти. Почему так??
Это в 64-х битах перед вызовом функции стак выравнивается по 16 байтам. Поэтому 8 байт на адрес возврата, остается ещё 8 (либо push rbp, либо sub rsp,8) — вот тебе и снова выравнивание по 16 байта.
В 32-х битах такого нет. Это либо под локальные переменные, либо х/з что за прикол.
В 32-х битах такого нет. Это либо под локальные переменные, либо х/з что за прикол.
ЕК
Однако calling convention'ы почему то требуют 16 байт на фрейм
Это где такое требование?
U
Это где такое требование?
не помню в каком CC
U
но было
DV
#abi
2.2.2 The Stack FrameIn addition to registers, each function has a frame on the run-time stack. This stackgrows downwards from high addresses. Table 2.2 shows the stack organization.The end of the input argument area shall be aligned on a 16 (32, if__m256ispassed on stack) byte boundary. In other words, the value(%esp+ 4)is alwaysa multiple of16(32) when control is transferred to the function entry point. Thestack pointer,%esp, always points to the end of the latest allocated stack frame.
https://www.uclibc.org/docs/psABI-i386.pdf
2.2.2 The Stack FrameIn addition to registers, each function has a frame on the run-time stack. This stackgrows downwards from high addresses. Table 2.2 shows the stack organization.The end of the input argument area shall be aligned on a 16 (32, if__m256ispassed on stack) byte boundary. In other words, the value(%esp+ 4)is alwaysa multiple of16(32) when control is transferred to the function entry point. Thestack pointer,%esp, always points to the end of the latest allocated stack frame.
https://www.uclibc.org/docs/psABI-i386.pdf
RG
Это в 64-х битах перед вызовом функции стак выравнивается по 16 байтам. Поэтому 8 байт на адрес возврата, остается ещё 8 (либо push rbp, либо sub rsp,8) — вот тебе и снова выравнивание по 16 байта.
В 32-х битах такого нет. Это либо под локальные переменные, либо х/з что за прикол.
В 32-х битах такого нет. Это либо под локальные переменные, либо х/з что за прикол.
Спасибо !
RG
Это в 64-х битах перед вызовом функции стак выравнивается по 16 байтам. Поэтому 8 байт на адрес возврата, остается ещё 8 (либо push rbp, либо sub rsp,8) — вот тебе и снова выравнивание по 16 байта.
В 32-х битах такого нет. Это либо под локальные переменные, либо х/з что за прикол.
В 32-х битах такого нет. Это либо под локальные переменные, либо х/з что за прикол.
в энтрипоинте у нас запушен адрес возврата?
ЕК
в энтрипоинте у нас запушен адрес возврата?
В винде нет, насколько я знаю (а вот в потоках вроде да). В линуксе запушены параметры, переменные окружения и ещё что-то там, т.е. считай, что нет
s
В винде нет, насколько я знаю (а вот в потоках вроде да). В линуксе запушены параметры, переменные окружения и ещё что-то там, т.е. считай, что нет
А в винде бывает код без потоков?