LpcSendWaitReceivePort

NTSTATUS __fastcall LpcSendWaitReceivePort(
        INT64 a1,
        INT64 a2,
        __m256i *a3,
        UINT64 a4,
        INT64 *WaitMode,
        INT64 *Alertable){
  _ETHREAD *CurrentThread; 
  NTSTATUS v7; 
  INT8 v9; 

  CurrentThread = (_ETHREAD *)KeGetCurrentThread();
  --CurrentThread->Tcb.KernelApcDisable;
  v7 = AlpcpProcessSynchronousRequest(
         (_ALPC_PORT *)a1,
         (unsigned int)a2 | 2,
         a3->m256i_i32,
         0i64,
         (PORT_MESSAGE *)a4,
         (UINT64 *)WaitMode,
         0i64,
         (_LARGE_INTEGER *)Alertable,
         0,
         v9);
  if( v7 == -1073740029 )
    v7 = -1073741769;
  if( v7 == -1073740031 )
    v7 = -1073741229;
  KeLeaveCriticalRegion();
  return v7;
}

Referenced by:

DbgkpSendApiMessageLpc
ExpRaiseHardError
IopSendMessageToTrackService