В рейтинге участвует:

групп:

каналов:

Виртуальный сервер на SSD - недорого!

Аренда выделенных и виртуальных серверов (VDS/VPS), хостинг, аренда IP-адресов, администрирование, круглосуточная поддержка

qwarta.ru подробнее

Резервное копирование с проверкой на вирусы!!!

Удобный сервис создания резервных копий на любой сервер сети интернет. Отслеживайте изменения, проверяйте на вирусы. Надежно защитите свой бизнес!

go.backupland.com

Выбираете сервер? Любая конфигурация на заказ!

Аренда физических серверов любых конфигураций под любые запросы - 1С бухгалтерия, игровые сервера, нагруженные проекты, интернет-магазины!

qwarta.ru подробнее

Size: a a a

rust_offtopic

352 membersпожаловаться на группу
2020 February 17

MB

Mikail Bagishov in rust_offtopic
Слава
Я немного не понимаю, что такое выравнивание стека при вызове. Мы в стек кладём значения. Например, я сделал push al, и в стеке оказался 1 байт. Что должно быть выровненным?
В момент, когда ты делаешь call, соглашение о вызове требует что-то про стек. например чтобы вершина стека была кратна 16
источник
22:11пожаловаться#1

С

Слава in rust_offtopic
Bogdan
ну падинг, чтобы поинтры лежили по адресам кратным 8
Поинтеры. То есть, если я засовываю в стек 1 байт, то потом для помещения в стек поинтера в 8 байт я должен перед ним засунуть в стек 7 нулей. Так?
источник
22:12пожаловаться#2

MB

Mikail Bagishov in rust_offtopic
Да
источник
22:12пожаловаться#3

С

Слава in rust_offtopic
Тогда это делает вызывающий.
источник
22:12пожаловаться#4

MB

Mikail Bagishov in rust_offtopic
Только это уже не ABI а требования архитектуры
источник
22:12пожаловаться#5

С

Слава in rust_offtopic
Не помню я таких требований, с другой стороны я только под DOS на ассемблере писал
источник
22:13пожаловаться#6

B

Bogdan in rust_offtopic
Слава
Не помню я таких требований, с другой стороны я только под DOS на ассемблере писал
вобще х86 может читать не выровнянные данные, только медленнее
источник
22:14пожаловаться#7

А⚙

Антон ⚙️ in rust_offtopic
Gymmasssorla
Rewrite It In Rust
Чёрт, чат обновился прям перед кликом — и вот я сбросил счётчик непрочитанных сообщений. Аргх!
источник
22:14пожаловаться#8

B

Bogdan in rust_offtopic
и атомарные операции будут не атомарно работать
источник
22:14пожаловаться#9

MB

Mikail Bagishov in rust_offtopic
https://stackoverflow.com/questions/49391001/why-does-system-v-amd64-abi-mandate-a-16-byte-stack-alignment
Stack Overflow
Why does System V / AMD64 ABI mandate a 16 byte stack alignment?
I've read in different places that it is done for "performance reasons", but I still wonder what are the particular cases where performance get improved by this 16-byte alignment. Or, in any case, ...
источник
22:16пожаловаться#10

B

Bogdan in rust_offtopic
The end of the input argument area shall be aligned on a 16 (32 or 64, if __m256 or __m512 is passed on stack) byte boundary. In other words, the value (%rsp + 8) is always a multiple of 16 (32 or 64) when control is transferred to the function entry point.
источник
22:17пожаловаться#11

B

Bogdan in rust_offtopic
сурс https://software.intel.com/sites/default/files/article/402129/mpx-linux64-abi.pdf
источник
22:17пожаловаться#12

С

Слава in rust_offtopic
По-моему, это как-то связано с размером блока виртуальной памяти. Там либо 16 байт минимальной гранулярности, либо 16 килобайт при установленном множителе. Хотя я это уже очень смутно помню.
источник
22:19пожаловаться#13

B

Bogdan in rust_offtopic
не, это связано с тем что mmx регистры 128 бит, т.е. 16 байт
источник
22:21пожаловаться#14

B

Bogdan in rust_offtopic
Слава
По-моему, это как-то связано с размером блока виртуальной памяти. Там либо 16 байт минимальной гранулярности, либо 16 килобайт при установленном множителе. Хотя я это уже очень смутно помню.
4 килобайта, или 1 Гб если включены Huge Pages
источник
22:21пожаловаться#15

MB

Mikail Bagishov in rust_offtopic
Или 2 МБ.
источник
22:22пожаловаться#16

B

Bogdan in rust_offtopic
хотя лучше былобы 16 кб хотябы в 64 битном режиме, хз чего оставили 4 кб (((
источник
22:22пожаловаться#17

B

Bogdan in rust_offtopic
хмммм, не знал)
источник
22:22пожаловаться#18

B

Bogdan in rust_offtopic
источник
22:24пожаловаться#19

B

Bogdan in rust_offtopic
эххх, такую архитектуру просрали — ia64
источник
22:24пожаловаться#20