6.62.41 x86 Защита потока управления Встроенные функции

Функция CET: ret_type _get_ssp (void)

Получить текущее значение указателя теневого стека, если поддержка теневого стека от Intel CET включена в оборудовании, или 0 в противном случае. ret_type составляет unsigned long long для 64-битных целей и unsigned int для 32-битных целей.

Функция CET: void _inc_ssp (unsigned int)

Увеличить текущий указатель теневого стека на размер, указанный аргументом функции. Аргумент маскируется до байтового значения по соображениям безопасности, поэтому для увеличения более чем на 255 байт необходимо вызывать функцию несколько раз.

Код разворачивания теневого стека выглядит следующим образом:

#include <immintrin.h>

/* Unwind the shadow stack for EH.  */
#define _Unwind_Frames_Extra(x)       \
  do                                  \
    {                                \
      _Unwind_Word ssp = _get_ssp (); \
      if (ssp != 0)                   \
        {                            \
          _Unwind_Word tmp = (x);     \
          while (tmp > 255)           \
            {                        \
              _inc_ssp (tmp);         \
              tmp -= 255;             \
            }                        \
          _inc_ssp (tmp);             \
        }                            \
    }                                \
    while (0)

Этот код выполняется безусловно на всех 64-битных процессорах. Для 32-битных процессоров код выполняется на тех, которые поддерживают многобайтовые инструкции NOP.