اصطلاحات استدعاء x86

يُعدّ cdecl cdecl(اختصارًا لـ C declaration ) اصطلاحًا لاستدعاء الدوال في لغة البرمجة C، ويستخدمه العديد من مُجمّعات C لبنية x86 . ^{[ 1 ]} في cdecl، تُمرّر وسائط الدوال الفرعية عبر المكدس . إذا كانت القيم المُعادة أعدادًا صحيحة أو عناوين ذاكرة، يضعها المُستدعى في المُسجّل EAX ، بينما تُوضع قيم الفاصلة العائمة في المُسجّل ST0 x87 . يحتفظ المُستدعي بالمُسجّلات EAX وECX وEDX، بينما يحتفظ المُستدعى بالمُسجّلات الأخرى. يجب أن تكون مُسجّلات الفاصلة العائمة x87 من ST0 إلى ST7 فارغة (مُحرّرة) عند استدعاء دالة جديدة، ويجب أن تكون من ST1 إلى ST7 فارغة عند الخروج من دالة. يجب أن يكون ST0 فارغًا أيضًا عندما لا يُستخدم لإعادة قيمة.

في سياق لغة C، يتم دفع وسائط الدالة على المكدس بترتيب من اليمين إلى اليسار (RTL)، أي يتم دفع الوسيط الأخير أولاً.

انظر إلى مقتطف الشفرة المصدرية التالية المكتوبة بلغة C :

int callee ( int , int , int );int المتصل ( void ) { إرجاع المستدعي ( 1 , 2 , 3 ) + 5 ; }

على معالجات x86 ، قد ينتج عنه كود التجميع التالي ( بصيغة Intel ):

المُستدعي: ; إنشاء إطار استدعاء جديد ; (قد تُنتج بعض المُترجمات تعليمة 'enter' بدلاً من ذلك) push ebp ; حفظ إطار الاستدعاء القديم mov ebp , esp ; تهيئة إطار الاستدعاء الجديد ; دفع وسائط الاستدعاء، بترتيب عكسي ; (قد تطرح بعض المُترجمات المساحة المطلوبة من مؤشر المكدس، ; ثم تكتب كل وسيط مباشرةً، انظر أدناه. ; يمكن لتعليمة 'enter' أيضًا القيام بشيء مماثل) ; sub esp, 12 : يمكن لتعليمة 'enter' القيام بذلك نيابةً عنا ; mov [ebp-4], 3 : أو mov [esp+8], 3 ; mov [ebp-8], 2 : أو mov [esp+4], 2 ; mov [ebp-12], 1 : أو mov [esp], 1 push 3 push 2 push 1 call callee ; استدعاء الروتين الفرعي 'callee' add esp , 12 ; إزالة وسائط الاستدعاء من الإطار، إضافة eax ، 5 ؛ تعديل نتيجة الروتين الفرعي ؛ (eax هي القيمة المرجعة من الدالة المستدعاة ، لذا لسنا بحاجة إلى نقلها إلى متغير محلي) ؛ استعادة إطار الاستدعاء القديم ؛ (قد تُنتج بعض المُترجمات تعليمة "مغادرة" بدلاً من ذلك) ؛ تُملي معظم اصطلاحات الاستدعاء أن يتم حفظ ebp بواسطة الدالة المستدعاة، أي أنه يتم الاحتفاظ به بعد استدعاء الدالة المستدعاة. لذلك، فإنه لا يزال يُشير إلى بداية إطار المكدس. نحتاج إلى التأكد من أن الدالة المستدعاة لا تُعدّل (أو تستعيد) ebp، لذا نحتاج إلى التأكد من أنها تستخدم اصطلاح استدعاء يقوم بذلك. إزالة ebp ؛ استعادة إطار الاستدعاء القديم، ret ؛ إرجاع

يقوم المستدعي بتنظيف المكدس بعد عودة استدعاء الدالة.

عادةً ما يكون اصطلاح الاستدعاء cdeclهو الاصطلاح الافتراضي لمترجمات لغة C x86 ، على الرغم من أن العديد من المترجمات توفر خيارات لتغيير اصطلاحات الاستدعاء المستخدمة تلقائيًا. لتعريف دالة يدويًا لتكون cdecl، يدعم بعضها الصيغة التالية:

return_type __cdecl func_name ();

يشبه هذا الأمر cdecl من حيث أن الوسائط تُدفع من اليمين إلى اليسار. مع ذلك، لا يتم الاحتفاظ بقيم EAX وECX وEDX، ويتم تمرير حجم قائمة المعاملات بالكلمات المزدوجة في AL.

Syscall هو اصطلاح الاستدعاء القياسي لواجهة برمجة تطبيقات نظام التشغيل OS/2 ذات 32 بت .

تُمرَّر الوسائط من اليمين إلى اليسار. تُمرَّر الوسائط الثلاثة الأولى (الأيسر) في السجلات EAX وEDX وECX، بينما تُمرَّر أربعة وسائط من نوع الفاصلة العائمة كحد أقصى في السجلات ST0 إلى ST3، مع العلم أنه يتم حجز مساحة لها في قائمة الوسائط على المكدس. تُعاد النتائج في السجل EAX أو ST0. ويتم الاحتفاظ بالسجلات EBP وEBX وESI وEDI.

يستخدم برنامج Optlink بواسطة مترجمات IBM VisualAge .

استنادًا إلى اصطلاح استدعاء لغة Borland Turbo Pascal ، يتم دفع المعلمات على المكدس بترتيب من اليسار إلى اليمين (LTR) (عكس cdecl)، ويكون المستدعى مسؤولاً عن إزالتها من المكدس.

يتم إرجاع النتيجة على النحو التالي:

• يتم إرجاع القيم الترتيبية في AL ( قيم 8 بت )، AX (قيم 16 بت)، EAX ( قيم 32 بت )، أو DX:AX (قيم 32 بت على أنظمة 16 بت).
• يتم إرجاع القيم الحقيقية في DX:BX:AX.
• يتم إرجاع قيم الفاصلة العائمة (8087) في ST0.
• يتم إرجاع المؤشرات في EAX على أنظمة 32 بت وفي AX على أنظمة 16 بت.
• يتم إرجاع السلاسل النصية في موقع مؤقت يشير إليه @Result الرمز.

كان هذا الأسلوب في استدعاء الدوال شائعًا في واجهات برمجة التطبيقات ذات 16 بت التالية: OS/2 1.x، و Microsoft Windows 3.x، و Borland Delphi الإصدار 1.x. تستخدم الإصدارات الحديثة من واجهة برمجة تطبيقات Windows الدالة stdcall ، والتي لا تزال تقوم باستعادة المكدس كما في أسلوب باسكال، ولكن يتم الآن دفع المعاملات من اليمين إلى اليسار.

يُعدّ اصطلاح استدعاء stdcall ^{[ 5 ]} شكلاً مُعدّلاً من اصطلاح استدعاء باسكال، حيث يكون المُستدعى مسؤولاً عن تنظيف المكدس، ولكن تُضاف المعاملات إلى المكدس بترتيب من اليمين إلى اليسار، كما هو الحال في اصطلاح استدعاء _cdecl. تُخصّص السجلات EAX وECX وEDX للاستخدام داخل الدالة. تُخزّن القيم المُعادة في السجل EAX.

stdcall هو اصطلاح الاستدعاء القياسي لواجهة برمجة تطبيقات Microsoft Win32 ولـ Open Watcom C++ .

تُمرر اصطلاحات Microsoft __fastcall أول وسيطين مناسبين (يتم تقييمهما من اليسار إلى اليمين) إلى ECX وEDX. ^{[ 6 ]} تُدفع الوسائط المتبقية إلى المكدس من اليمين إلى اليسار. عند قيام المُصرّف بالتجميع لـ IA64 أو AMD64 ، فإنه يتجاهل الكلمة المفتاحية __fastcall (أو أي كلمة مفتاحية أخرى لاصطلاحات الاستدعاء باستثناء __vectorcall ) ويستخدم اصطلاح الاستدعاء الافتراضي لـ Microsoft ذي 64 بت بدلاً من ذلك.

توفر مُجمّعات أخرى مثل GCC ^{[ 7 ]} و Clang ^{[ 8 ]} اصطلاحات استدعاء "fastcall" مماثلة، على الرغم من أنها ليست بالضرورة متوافقة مع بعضها البعض أو مع fastcall من Microsoft. ^{[ 9 ]}

انظر إلى مقتطف الشفرة التالي بلغة C:

__attribute__ (( fastcall )) void printnums ( int num1 , int num2 , int num3 ){ printf ( "الأرقام التي أرسلتها هي: %d %d %d" , num1 , num2 , num3 ); }int main (){ printnums ( 1 , 2 , 3 ); return 0 ; }

سيبدو فك تجميع الدالة الرئيسية باستخدام x86 كما يلي (بصيغة Intel):

main: ; إعداد المكدس push ebp mov ebp , esp push 3 ; القيمة الفورية 3 (يتم دفع الوسيط الثالث إلى المكدس) mov edx , 0x2 ; القيمة الفورية 2 (يتم نسخ الوسيط الثاني) إلى سجل edx. mov ecx , 0x1 ; القيمة الفورية 1 (يتم نسخ الوسيط الأول) إلى سجل ecx. call printnums mov eax , 0 ; return 0 leave retn

يتم تمرير الوسيطين الأولين من اليسار إلى اليمين، ويُضاف الوسيط الثالث إلى المكدس. لا توجد عملية تنظيف للمكدس، حيث يتم ذلك بواسطة الدالة المستدعاة. تفكيك الدالة المستدعاة هو:

printnums: ; إعداد المكدس push ebp mov ebp , esp sub esp , 0x08 mov [ ebp-0x04 ], ecx ; في x86، ecx = الوسيط الأول. mov [ ebp-0x08 ], edx ; arg2 push [ ebp + 0x08 ] ; يتم دفع arg3 إلى المكدس. push [ ebp-0x08 ] ; يتم دفع arg2 push [ ebp-0x04 ] ; يتم دفع arg1 push 0x8065d67 ; "الأرقام التي أرسلتها هي %d %d %d" call printf ; تنظيف المكدس add esp , 0x10 nop leave retn 0x04

بما أن الوسيطين تم تمريرهما عبر السجلات وتم دفع معلمة واحدة فقط في المكدس، فإن القيمة المدفوعة يتم مسحها بواسطة تعليمة retn، حيث أن حجم int هو 4 بايت في أنظمة x86.

في Visual Studio 2013، قدمت مايكروسوفت اصطلاح استدعاء __vectorcall استجابةً لمخاوف الكفاءة لدى مطوري الألعاب والرسومات والفيديو/الصوت وبرامج الترميز. يسمح هذا النظام بتمرير أنواع المتجهات الأكبر ( float ، double ، __m128 ، __m256 ) في السجلات بدلاً من تمريرها عبر المكدس. ^{[ 10 ]}

تُضيف الدالة __vectorcall دعمًا لتمرير قيم التجميع المتجانس للمتجهات (HVA)، وهي أنواع مركبة (هياكل) تتكون حصريًا من أربعة أنواع متجهات متطابقة كحد أقصى، باستخدام نفس السجلات الستة. بعد تخصيص السجلات لوسائط نوع المتجه، تُخصص السجلات غير المستخدمة لوسائط HVA من اليسار إلى اليمين. وتظل قواعد التموضع سارية. تُعاد قيم نوع المتجه وHVA الناتجة باستخدام أول أربعة سجلات XMM/YMM. ^{[ 11 ]}

بالنسبة لبرامج IA-32 و x64، فإن الدالة __vectorcall تُشابه الدالة __fastcall واتفاقيات استدعاء x64 الأصلية على التوالي، ولكنها تُوسّعها لدعم تمرير وسائط المتجهات باستخدام سجلات SIMD . في IA-32، تُمرّر القيم الصحيحة كالمعتاد، وتحتفظ سجلات SIMD الستة الأولى ( XMM / YMM 0-5) بما يصل إلى ست قيم من نوع الفاصلة العائمة أو المتجهات أو HVA بالتسلسل من اليسار إلى اليمين، بغض النظر عن المواضع الفعلية الناتجة عن، على سبيل المثال، وجود وسيط عدد صحيح بينها. أما في x64، فلا تزال قاعدة اتفاقية x64 الأصلية سارية، بحيث لا تحتفظ سجلات XMM/YMM 0-5 إلا بوسائط الفاصلة العائمة أو المتجهات أو HVA عندما تكون من الأول إلى السادس. ^{[ 11 ]}

كما يقوم كل من مترجم Clang ومترجم Intel C++ بتنفيذ vectorcall. ^{[ 12 ]}

تتعامل دالة vectorcall فقط مع عرض سجلات المتجهات ذي 256 بت (AVX، YMM). وهي لا تغطي عرض AVX-512 (ZMM).

قبل استخدام __vectorcall، كان لدى ICC اصطلاح مشابه يُسمى __regcall ، حيث يتم تخزين أكبر عدد ممكن من المعاملات في السجلات. ^{[ 13 ] [ 14 ]} وهو مدعوم أيضًا من قِبل clang. ^{[ 12 ]}

لدى إنتل واجهة برمجة تطبيقات (ABI) لوظائف المتجهات تعتمد على __regcall، وهي غير مُطبقة بواسطة clang (حتى نوفمبر 2025). تتعامل هذه الواجهة مع متجهات من أنواع البيانات العادية، لذا يتم تمرير معظم المعاملات (وإرجاع النتائج) عبر سجلات [XYZ]MM. ^{[ 15 ]} وقد اعتمدت مكتبة libmvec التابعة لـ glibc صيغةً معدلةً من هذه الواجهة، تستخدم اصطلاح استدعاء System V المعتاد لمنصة x86_64 فيما يتعلق باستخدام السجلات، وهي مدعومة من قِبل GCC وClang وICC. ^{[ 16 ]}

في أنظمة x86 ذات 32 بت، يحتوي نظام GNU على خاصية regparm التي تسمح بتمرير ما يصل إلى ثلاثة معلمات غير متغيرة في EAX وEDX وECX. وهي ليست اصطلاح استدعاء خاص بها بقدر ما هي تعديل يمكن تطبيقه على اصطلاحات الاستدعاء الموجودة. ^{[ 12 ]}

يحتوي Clang على مُعدِّلات اصطلاحية مماثلة، مثل preserve_all و preserve_none و preserve_most ، وهي قابلة للتطبيق على نطاق واسع على العديد من البنى. ^{[ 12 ]} يدعم GCC هذه المُعدِّلات على معماريتي x86 و x86-64. ^{[ 17 ]}preserve_none

بتقييم الوسائط من اليسار إلى اليمين، يمرر ثلاثة وسائط عبر EAX وEDX وECX. تُضاف الوسائط المتبقية إلى المكدس، أيضًا من اليسار إلى اليمين. ^{[ 18 ]} هذه هي اصطلاحية الاستدعاء الافتراضية لمترجم دلفي ذي 32 بت ، حيث تُعرف باسم register . تُستخدم هذه الاصطلاحية أيضًا في C++Builder من Embarcadero ، حيث تُسمى __fastcall . ^{[ 19 ]} في هذا المترجم، يمكن استخدام fastcall من Microsoft باسم __msfastcall . ^{[ 20 ]}

يمكن جعل كل من GCC وClang يستخدمان اصطلاح استدعاء مماثلًا باستخدام __stdcallسمة regparmالدالة أو -mregparm=3المُبدِّل. (يتم عكس ترتيب المكدس). من الممكن أيضًا إنشاء نسخة مُعدّلة لتنظيف المُستدعي باستخدام cdeclأو توسيع هذا ليشمل استخدام سجلات SSE أيضًا. ^{[ 21 ]}cdecl يستخدم نواة لينكس على معالجات i386 إصدارًا قائمًا على هذا الاصطلاح منذ الإصدار 2.6.20 (الذي صدر في فبراير 2007) . ^{[ 22 ]}

لا يدعم Watcom الكلمة المفتاحية __fastcall إلا إذا تم تعريفها باسم بديل (null). يمكن تحديد اصطلاح استدعاء السجل عبر مفتاح سطر الأوامر.

يتم تخصيص ما يصل إلى 4 سجلات للوسائط بالترتيب التالي: EAX، EDX، EBX، ECX. تُخصص الوسائط للسجلات من اليسار إلى اليمين. إذا تعذر تخصيص أي وسيط لسجل (كأن يكون حجمه كبيرًا جدًا)، فإنه، مع جميع الوسائط اللاحقة، يُخصص للمكدس. تُدفع الوسائط المُخصصة للمكدس من اليمين إلى اليسار. تُشوّه الأسماء بإضافة شرطة سفلية لاحقة. تُنظف الدالة المُستدعِية المكدس. ^{[ 23 ]}

تعتمد الدوال ذات عدد متغير من الوسائط على اصطلاح الاستدعاء القائم على مكدس Watcom.

يستخدم مُصرّف Watcom C/C++ أيضًا التوجيه #pragma aux ^{[ 24 ]} الذي يسمح للمستخدم بتحديد اصطلاح الاستدعاء الخاص به. وكما هو مذكور في دليل المستخدم، "من غير المرجح أن يحتاج سوى عدد قليل جدًا من المستخدمين إلى هذه الطريقة، ولكن إذا دعت الحاجة إليها، فقد تكون منقذة".

تُمرَّر المعاملات الصحيحة الأربعة الأولى في المسجلات EAX وEBX وECX وEDX. أما معاملات الفاصلة العائمة فتُمرر عبر مكدس الفاصلة العائمة - المسجلات ST0 وST1 وST2 وST3 وST4 وST5 وST6. تُمرَّر معاملات البنية دائمًا عبر المكدس. تُمرَّر المعاملات المضافة عبر المكدس بعد استنفاد المسجلات. تُعاد القيم الصحيحة في EAX، والمؤشرات في EDX، وأنواع الفاصلة العائمة في ST0.

في دلفي وفري باسكال على نظام التشغيل مايكروسوفت ويندوز ، تُغلف اصطلاحات استدعاء الدالة safecall معالجة أخطاء COM ( نموذج كائن المكون )، وبالتالي لا يتم تسريب الاستثناءات إلى المُستدعي، بل يتم الإبلاغ عنها في قيمة HRESULT المُعادة، كما هو مطلوب في COM/OLE. عند استدعاء دالة safecall من كود دلفي، يتحقق دلفي تلقائيًا من قيمة HRESULT المُعادة ويُطلق استثناءً إذا لزم الأمر.

تُشابه آلية استدعاء safecall آلية استدعاء stdcall، باستثناء أن الاستثناءات تُعاد إلى المُستدعي في EAX كـ HResult (بدلاً من FS:[0])، بينما تُمرر نتيجة الدالة بالمرجع على المكدس كما لو كانت مُعامل "out" نهائي. عند استدعاء دالة Delphi من داخل Delphi، ستظهر آلية الاستدعاء هذه كأي آلية استدعاء أخرى، لأنه على الرغم من إعادة الاستثناءات في EAX، إلا أن المُستدعي يُحوّلها تلقائيًا إلى استثناءات صحيحة. عند استخدام كائنات COM المُنشأة بلغات أخرى، تُثار HResults تلقائيًا كاستثناءات، وتكون نتيجة دوال Get في النتيجة نفسها بدلاً من مُعامل. عند إنشاء كائنات COM في Delphi باستخدام safecall، لا داعي للقلق بشأن HResults، حيث يمكن إثارة الاستثناءات بشكل طبيعي ولكنها ستُعرض كـ HResults في اللغات الأخرى.

دالة اسم_الدالة ( أ : DWORD ) : DWORD ؛ استدعاء_آمن ؛

تُعيد هذه الدالة نتيجة وتُثير استثناءات مثل دالة دلفي العادية، ولكنها تُمرر القيم والاستثناءات كما لو كانت:

دالة اسم_الدالة ( أ : DWORD ؛ نتيجة الإخراج : DWORD ) : HResult ؛ استدعاء قياسي ؛

يُستخدم هذا الأسلوب لاستدعاء الدوال الأعضاء غير الثابتة في لغة C++. يوجد إصداران رئيسيان منه، thiscallيعتمدان على المُصرّف وما إذا كانت الدالة تستخدم عددًا متغيرًا من الوسائط أم لا.

بالنسبة لمترجم GCC، thiscallفإنّ هذا يكاد يكون مطابقًا لما يلي cdecl: يقوم المستدعي بتنظيف المكدس، ويتم تمرير المعاملات من اليمين إلى اليسار. الفرق هو إضافة المؤشر this، الذي يُدفع إلى المكدس أخيرًا، كما لو كان المعامل الأول في نموذج الدالة .

في مُصرّف Microsoft Visual C++، thisيُمرَّر المؤشر في ECX، وتتولى الدالة المُستدعاة تنظيف المكدس، مُحاكيةً بذلك الاصطلاح stdcallالمُستخدم في لغة C لهذا المُصرّف وفي دوال واجهة برمجة تطبيقات Windows. عندما تستخدم الدوال عددًا متغيرًا من الوسائط، تتولى الدالة المُستدعِية تنظيف المكدس (انظر المرجع cdecl).

لا يمكن تحديد اصطلاح الاستدعاء thiscallصراحةً إلا في Microsoft Visual C++ 2005 والإصدارات الأحدث. أما في أي مُصرّف آخر، فإن thiscall ليست كلمة مفتاحية. (مع ذلك، يجب على برامج تفكيك التعليمات البرمجية، مثل IDA ، تحديدها. لذا، يستخدم IDA الكلمة المفتاحية __thiscall لهذا الغرض).

وفقًا لـ Intel ABI الذي تتوافق معه الغالبية العظمى من المترجمات، يجب أن تكون EAX و EDX و ECX متاحة للاستخدام داخل إجراء أو وظيفة، ولا يلزم الاحتفاظ بها.

كما يوحي الاسم، فإن هذه السجلات ذات الأغراض العامة عادة ما تحتوي على معلومات مؤقتة (متطايرة)، والتي يمكن استبدالها بواسطة أي روتين فرعي.

لذلك، تقع على عاتق المتصل مسؤولية دفع كل من هذه السجلات إلى المكدس، إذا كان يرغب في استعادة قيمها بعد استدعاء روتين فرعي.

تُستخدم السجلات الأخرى للاحتفاظ بالقيم طويلة الأمد (غير المتطايرة)، والتي يجب الحفاظ عليها عبر الاستدعاءات.

بمعنى آخر، عندما يقوم المتصل باستدعاء إجراء، يمكنه أن يتوقع أن تحتفظ تلك السجلات بنفس القيمة بعد أن يعود المستدعى.

وبالتالي، تقع على عاتق المتلقي مسؤولية حفظ (إدخال البيانات في البداية) واستعادتها (إخراجها عند الحاجة) قبل العودة إلى المتصل. وكما في الحالة السابقة، ينبغي تطبيق هذه الممارسة فقط على السجلات التي يُجري عليها المتلقي تغييرات.

يُتبع اصطلاح استدعاء Microsoft x64 ^{[ 25 ] [ 26 ]} في نظام التشغيل Windows وواجهة UEFI قبل بدء التشغيل ( للوضع الطويل على معالجات x86-64 ). تُوضع الوسائط الأربعة الأولى في السجلات. أي RCX وRDX وR8 وR9 (بهذا الترتيب) لوسائط الأعداد الصحيحة أو البُنى أو المؤشرات، وXMM0 وXMM1 وXMM2 وXMM3 لوسائط الأعداد العشرية. تُضاف الوسائط إلى المكدس (من اليمين إلى اليسار). تُعاد قيم الأعداد الصحيحة (كما في x86) في RAX إذا كانت 64 بت أو أقل. تُعاد قيم الأعداد العشرية في XMM0. لا تُضاف أصفار إلى المعاملات التي يقل طولها عن 64 بت؛ أي لا تُصفّر البتات العليا. ^{[ 27 ]}

تُمرَّر وتُعاد البنى والاتحادات ذات الأحجام المطابقة للأعداد الصحيحة كما لو كانت أعدادًا صحيحة. وإلا، تُستبدل بمؤشر عند استخدامها كوسيط. عند الحاجة إلى إرجاع بنية ذات حجم زائد، يُضاف مؤشر آخر إلى مساحة يوفرها المستدعي كوسيط أول، مما يُزيح جميع الوسائط الأخرى إلى اليمين بمقدار خانة واحدة. يصبح هذا المؤشر أيضًا قيمة الإرجاع في RAX. ^{[ 28 ]}

عند التجميع لبنية x64 في سياق Windows (سواء باستخدام أدوات Microsoft أو أدوات غير تابعة لـ Microsoft)، فإن stdcall و thiscall و cdecl و fastcall كلها تحل إلى استخدام هذا الاصطلاح.

في اصطلاح استدعاء الدوال في نظام مايكروسوفت x64، تقع على عاتق المُستدعي مسؤولية تخصيص 32 بايت من "مساحة الظل" على المكدس قبل استدعاء الدالة مباشرةً (بغض النظر عن العدد الفعلي للمعاملات المستخدمة)، وإخراج البيانات من المكدس بعد الاستدعاء. تُستخدم مساحة الظل لتخزين قيم RCX وRDX وR8 وR9، ^{[ 29 ]} ولكن يجب إتاحتها لجميع الدوال، حتى تلك التي تحتوي على أقل من أربعة معاملات.

تُعتبر السجلات RAX وRCX وRDX وR8 وR9 وR10 وR11 متغيرة (محفوظة من قبل المتصل). ^{[ 30 ]}

تعتبر السجلات RBX، وRBP، وRDI، وRSI، وRSP، وR12، وR13، وR14، وR15 غير متطايرة (محفوظة باسم callee). ^{[ 30 ]}

على سبيل المثال، ستأخذ دالة تستقبل خمسة وسائط عددية صحيحة الوسائط من الأول إلى الرابع في سجلات، بينما يُضاف الوسيط الخامس إلى أعلى مساحة الظل. لذا، عند استدعاء الدالة، سيتكون المكدس (بترتيب تصاعدي) من عنوان الإرجاع، متبوعًا بمساحة الظل (32 بايت)، ثم الوسيط الخامس.

تتم محاذاة إطار المكدس إلى 16 بايت. ^{[ 31 ]}

يقوم برنامج Visual Studio 2008 بتخزين الأرقام العشرية في XMM6 و XMM7، بالإضافة إلى XMM8 حتى XMM15.

لا تستخدم اتفاقية الاستدعاء أجزاء YMM و ZMM من سجلات المتجهات لتمرير الوسائط والنتائج.

يُتبع اصطلاح استدعاء واجهة التطبيق الثنائية (ABI) الخاصة بنظام System V AMD64 في أنظمة Solaris و Linux و FreeBSD و macOS ، ^{[ 32 ]} وهو المعيار الفعلي بين أنظمة التشغيل Unix والأنظمة الشبيهة بـ Unix. يعتمد معيار استدعاء OpenVMS على معمارية x86-64 على واجهة التطبيق الثنائية (ABI) الخاصة بنظام System V مع بعض الإضافات اللازمة للتوافق مع الإصدارات السابقة. ^{[ 33 ]}

تُمرَّر الوسائط الستة الأولى، سواءً كانت أعدادًا صحيحة أو مؤشرات، في المسجلات RDI وRSI وRDX وRCX وR8 وR9 (يُستخدم R10 كمؤشر سلسلة ثابت في حالة الدوال المتداخلة ^{[ 34 ] : 21} )، بينما تُستخدم المسجلات XMM0 وXMM1 وXMM2 وXMM3 وXMM4 وXMM5 وXMM6 وXMM7 للوسائط العشرية الأولى. ^{[ 34 ] : 22} وكما هو الحال في اصطلاح استدعاء Microsoft x64، تُمرَّر الوسائط المُضافة عبر المكدس. ^{[ 34 ] : 22} تُخزَّن قيم الإرجاع الصحيحة التي يصل حجمها إلى 64 بت في RAX، بينما تُخزَّن القيم التي يصل حجمها إلى 128 بت في RAX وRDX. وبالمثل، تُخزَّن قيم الإرجاع العشرية في XMM0 وXMM1. ^{[ 34 ] : 25} تُستخدم المسجلات الأوسع YMM وZMM لتمرير وإرجاع قيم أوسع بدلاً من XMM عند وجودها. ^{[ 34 ] : 26، 55}

تُقسّم معلمات البنية والاتحاد التي يبلغ حجمها مؤشرين (ثمانية في حالة حقول SSE فقط) أو أقل، والمُحاذية لحدود 64 بت، إلى "ثمانية بايتات"، ويُصنّف كل منها ويُمرّر كمعلمة منفصلة، ​​طالما توفرت سجلات كافية. ^{[ 34 ] : 24} وإلا، تُمرّر في الذاكرة. تُعاد أنواع إرجاع البنية والاتحاد التي يبلغ حجمها مؤشرين أو أقل في RAX وRDX (أو XMM0 وXMM1). عند الحاجة إلى إرجاع بنية كبيرة الحجم، يُضاف مؤشر آخر إلى مساحة يُحددها المُستدعي كمعامل أول، مما يُزيح جميع المعاملات الأخرى إلى اليمين بمقدار خانة واحدة، وتُعاد قيمة هذا المؤشر في RAX. ^{[ 34 ] : 27}

إذا رغب المستدعى في استخدام السجلات RBX وRSP وRBP وR12-R15، فعليه استعادة قيمها الأصلية قبل إعادة التحكم إلى المستدعي. أما السجلات الأخرى، فيجب على المستدعي حفظها إذا رغب في الاحتفاظ بقيمها. ^{[ 34 ] : 16}

بالنسبة لدوال العقدة الطرفية (الدوال التي لا تستدعي أي دوال أخرى)، تُخزَّن مساحة بحجم 128 بايت أسفل مؤشر مكدس الدالة مباشرةً. تُسمى هذه المساحة " المنطقة الحمراء" . لن تُستبدل هذه المنطقة بواسطة أي معالجات إشارات أو مقاطعات. بالتالي، يمكن للمترجمات استخدام هذه المنطقة لحفظ المتغيرات المحلية. قد تُهمل المترجمات بعض التعليمات في بداية الدالة (مثل ضبط RSP وRBP) باستخدام هذه المنطقة. مع ذلك، قد تستبدل دوال أخرى هذه المنطقة. لذا، ينبغي استخدام هذه المنطقة فقط لدوال العقدة الطرفية، gccمع clangتوفير -mno-red-zoneخيار لتعطيل تحسينات المنطقة الحمراء.

إذا كانت الدالة المستدعاة دالة متغيرة الوسائط ، فيجب على المستدعي توفير عدد وسائط الفاصلة العائمة التي تم تمريرها إلى الدالة في سجلات المتجهات في سجل AL. ^{[ 34 ] : 55}

يتم محاذاة إطار المكدس افتراضيًا إلى حد 16 بايت. إذا __m256تم تمرير نوع (AVX) على المكدس، فيجب محاذاته إلى 32 بايت؛ وإذا __m512تم تمرير نوع (AVX512)، فيجب محاذاته إلى 64 بايت. ^{[ 34 ] : 22}

بخلاف اصطلاح استدعاء مايكروسوفت، لا يتم توفير مساحة ظل؛ عند دخول الدالة، يكون عنوان الإرجاع مجاورًا للوسيط الصحيح السابع على المكدس.

• ابتداءً من Visual Studio 2013، قدمت مايكروسوفت اصطلاح استدعاء __vectorcall ، الذي يُعد امتدادًا لاصطلاح x64. للاطلاع على وصف كامل، راجع قسم Microsoft vectorcall أعلاه. 
• سجل إنتل (انظر أعلاه).