uasm 1.0.9+2.57

/****************************************************************************
*
*  This code is Public Domain.
*
*  ========================================================================
*
* Description:  Processing of PROC/ENDP/LOCAL directives.
*
****************************************************************************/

#include <ctype.h>

#include "globals.h"
#include "memalloc.h"
#include "parser.h"
#include "segment.h"
#include "extern.h"
#include "equate.h"
#include "fixup.h"
#include "label.h"
#include "input.h"
#include "lqueue.h"
#include "tokenize.h"
#include "expreval.h"
#include "types.h"
#include "condasm.h"
#include "macro.h"
#include "proc.h"
#include "fastpass.h"
#include "listing.h"
#include "posndir.h"
#include "myassert.h"
#include "reswords.h"
#if AMD64_SUPPORT
#include "win64seh.h"
#endif

#ifdef __I86__
#define NUMQUAL (long)
#else
#define NUMQUAL
#endif

/* STACKPROBE: emit a conditional "call __chkstk" inside the prologue
* if stack space that is to be allocated exceeds 1000h bytes.
* this is currently implemented for 64-bit only,
* if OPTION FRAME:AUTO is set and the procedure has the FRAME attribute.
* it's not active by default because, in a few cases, the listing might get messed.
*/
#define STACKPROBE 0

extern const char szDgroup[];
extern uint_32 list_pos;  /* current LST file position */
extern unsigned char regsize[6];
/*
* Masm allows nested procedures
* but they must NOT have params or locals
*/

/*
* calling convention FASTCALL supports:
* - Watcom C: registers e/ax,e/dx,e/bx,e/cx
* - MS fastcall 16-bit: registers ax,dx,bx (default for 16bit)
* - MS fastcall 32-bit: registers ecx,edx (default for 32bit)
* - Win64: registers rcx, rdx, r8, r9 (default for 64bit)
*/

struct dsym             *CurrProc;      /* current procedure */
int                     procidx;        /* procedure index */
int                     CurrProcLine;
int XYZMMsize;
static struct proc_info *ProcStack;

/* v2.11: ProcStatus replaced DefineProc */
enum proc_status ProcStatus;

#if AMD64_SUPPORT
static bool             endprolog_found;
static uint_8           unw_segs_defined;
static UNWIND_INFO      unw_info;
static UNWIND_CODE      unw_code[258];	/* 255 is the max */
#endif

#if AMD64_SUPPORT
										/* @ReservedStack symbol; used when option W64F_AUTOSTACKSP has been set */
struct asym *sym_ReservedStack; /* max stack space required by INVOKE */
#endif

								/* tables for FASTCALL support */

								/* v2.07: 16-bit MS FASTCALL registers are AX, DX, BX.
								* And params on stack are in PASCAL order.
								*/
								//static const enum special_token ms32_regs16[] = { T_CX, T_DX };
static const enum special_token ms32_regs16[] = { T_AX, T_DX, T_BX };
static const enum special_token ms32_regs32[] = { T_ECX,T_EDX };
static const enum special_token delphi_regs32[] = { T_EAX, T_EDX, T_ECX, };

/* v2.07: added */
static const int ms32_maxreg[] = {
	sizeof(ms32_regs16) / sizeof(ms32_regs16[0]),
	sizeof(ms32_regs32) / sizeof(ms32_regs32[0]),
};

static const int delphi_maxreg[] = {
	sizeof(delphi_regs32) / sizeof(delphi_regs32[0]),
	sizeof(delphi_regs32) / sizeof(delphi_regs32[0]),
};

#if OWFC_SUPPORT
static const enum special_token watc_regs8[] = { T_AL, T_DL, T_BL, T_CL };
static const enum special_token watc_regs16[] = { T_AX, T_DX, T_BX, T_CX };
static const enum special_token watc_regs32[] = { T_EAX, T_EDX, T_EBX, T_ECX };
static const enum special_token watc_regs_qw[] = { T_AX, T_BX, T_CX, T_DX };
#endif

#if AMD64_SUPPORT

static const enum special_token ms64_regs[] = { T_RCX, T_RDX, T_R8, T_R9 };

static const enum special_token sysV64_regs[] = { T_RDI, T_RSI, T_RDX, T_RCX, T_R8, T_R9 };
static const enum special_token sysV64_regs32[] = { T_EDI, T_ESI, T_EDX, T_ECX, T_R8D, T_R9D };
static const enum special_token sysV64_regs16[] = { T_DI, T_SI, T_DX, T_CX, T_R8W, T_R9W };
static const enum special_token sysV64_regs8[] = { T_DIL, T_SIL, T_DL, T_CL, T_R8B, T_R9B };
static const enum special_token sysV64_regsXMM[] = { T_XMM0, T_XMM1, T_XMM2, T_XMM3, T_XMM4, T_XMM5, T_XMM6, T_XMM7 };
static const enum special_token sysV64_regsYMM[] = { T_YMM0, T_YMM1, T_YMM2, T_YMM3, T_YMM4, T_YMM5, T_YMM6, T_YMM7 };
static const enum special_token sysV64_regsZMM[] = { T_ZMM0, T_ZMM1, T_ZMM2, T_ZMM3, T_ZMM4, T_ZMM5, T_ZMM6, T_ZMM7 };

/* win64 non-volatile GPRs: T_RBX, T_RBP, T_RSI, T_RDI, T_R12, T_R13, T_R14, T_R15 */
static const uint_16 win64_nvgpr = 0xF0E8;

/* win64 non-volatile XMM regs: XMM6-XMM15 */
static const uint_16 win64_nvxmm = 0xFFC0;

static const int sysv_maxreg[] = {
	sizeof(sysV64_regs) / sizeof(sysV64_regs[0]),
	sizeof(sysV64_regs) / sizeof(sysV64_regs[0]),
};

#endif


struct fastcall_conv {
	int(*paramcheck)(struct dsym *, struct dsym *, int *);
	void(*handlereturn)(struct dsym *, char *buffer);
};

struct vectorcall_conv {
	int(*paramcheck)(struct dsym *, struct dsym *, int *);
	void(*handlereturn)(struct dsym *, char *buffer);
};

struct sysvcall_conv {
	int(*paramcheck)(struct dsym *, struct dsym *, int *, int *);
	void(*handlereturn)(struct dsym *, char *buffer);
};

struct delphicall_conv {
	int(*paramcheck)(struct dsym *, struct dsym *, int *);
	void(*handlereturn)(struct dsym *, char *buffer);
};


static  int ms32_pcheck(struct dsym *, struct dsym *, int *);
static void ms32_return(struct dsym *, char *);

#if OWFC_SUPPORT
static  int watc_pcheck(struct dsym *, struct dsym *, int *);
static void watc_return(struct dsym *, char *);
#endif

#if AMD64_SUPPORT
static  int ms64_pcheck(struct dsym *, struct dsym *, int *);
static void ms64_return(struct dsym *, char *);
#endif

#if SYSV_SUPPORT
static  int sysv_pcheck(struct dsym *, struct dsym *, int *, int *);
static void sysv_return(struct dsym *, char *);
#endif

#if DELPHI_SUPPORT
static  int delphi_pcheck(struct dsym *, struct dsym *, int *);
static void delphi_return(struct dsym *, char *);
#endif

static void check_proc_fpo(struct proc_info *);

/* table of fastcall types.
* must match order of enum fastcall_type!
* also see table in mangle.c!
*/

static const struct fastcall_conv fastcall_tab[] = {
	{ ms32_pcheck, ms32_return },  /* FCT_MSC */
#if OWFC_SUPPORT
	{ watc_pcheck, watc_return },  /* FCT_WATCOMC */
#endif
#if AMD64_SUPPORT
	{ ms64_pcheck, ms64_return }   /* FCT_WIN64 */
#endif
};

static const struct vectorcall_conv vectorcall_tab[] = {
	{ ms32_pcheck, ms32_return },  /* FCT_MSC */
#if OWFC_SUPPORT
	{ watc_pcheck, watc_return },  /* FCT_WATCOMC */
#endif
#if AMD64_SUPPORT
	{ ms64_pcheck, ms64_return }   /* FCT_WIN64 */
#endif
};

static const struct sysvcall_conv sysvcall_tab[] = {
	{ ms32_pcheck, ms32_return },  /* FCT_MSC */
#if OWFC_SUPPORT		
	{ watc_pcheck, watc_return },  /* FCT_WATCOMC */
#endif		
#if SYSV_SUPPORT		
	{ sysv_pcheck, sysv_return }   /* FCT_WIN64 / SYSTEMV */
#endif		
};

static const struct delphicall_conv delphicall_tab[] = {
	{ delphi_pcheck, delphi_return },   /* FCT_MSC / DELPHI */
#if OWFC_SUPPORT
	{ watc_pcheck, watc_return },		/* FCT_WATCOMC */
#endif
#if AMD64_SUPPORT
	{ ms64_pcheck, ms64_return }		/* FCT_WIN64 */
#endif
};

const enum special_token stackreg[] = { T_SP, T_ESP,
#if AMD64_SUPPORT
T_RSP
#endif
};

#if STACKBASESUPP==0
const enum special_token basereg[] = {
	T_BP, T_EBP,
#if AMD64_SUPPORT
	T_RBP
#endif
};
#else
uint_32 StackAdj;  /* value of @StackBase variable */
int_32 StackAdjHigh;
#endif

#if AMD64_SUPPORT
static const char * const fmtstk0[] = {
	"sub %r, %d",
	"%r %d",
#if STACKPROBE
	"mov %r, %d",
#endif
};
static const char * const fmtstk1[] = {
	"sub %r, %d + %s",
	"%r %d + %s",
#if STACKPROBE
	"mov %r, %d + %s",
#endif
};

static const char * const fmtstk2[] = {
	"lea %r, [%r + %d]",
};
static const char * const fmtstk3[] = {
	"lea %r, [%r + %d + %s]",
};
#endif

#define ROUND_UP( i, r ) (((i)+((r)-1)) & ~((r)-1))

/* Declare proc functions */
static void SetLocalOffsets_RSP(struct proc_info *info);
static void SetLocalOffsets_RBP(struct proc_info *info);
static void pop_register(uint_16 *regist);
static void WriteSEHData(struct dsym *proc);

static void SetLocalOffsets_RBP_SYSV(struct proc_info* info);

#if OWFC_SUPPORT
/* register usage for OW fastcall (register calling convention).
* registers are used for parameter size 1,2,4,8.
* if a parameter doesn't fit in a register, a register pair is used.
* however, valid register pairs are e/dx:e/ax and e/cx:e/bx only!
* if a parameter doesn't fit in a register pair, registers
* are used ax:bx:cx:dx!!!
* stack cleanup for OW fastcall: if the proc is VARARG, the caller
* will do the cleanup, else the called proc does it.
* in VARARG procs, all parameters are pushed onto the stack!
*/
static int watc_pcheck(struct dsym *proc, struct dsym *paranode, int *used)
/***************************************************************************/
{
	static char regname[64];
	static char regist[32];
	int newflg;
	int shift;
	int firstreg;
	uint_8 Ofssize = GetSymOfssize(&proc->sym);
	int size = SizeFromMemtype(paranode->sym.mem_type, paranode->sym.Ofssize, paranode->sym.type);

	/* v2.05: VARARG procs don't have register params */
	if (proc->e.procinfo->has_vararg)
		return(0);

	if (size != 1 && size != 2 && size != 4 && size != 8)
		return(0);

	/* v2.05: rewritten. The old code didn't allow to "fill holes" */
	if (size == 8) {
		newflg = Ofssize ? 3 : 15;
		shift = Ofssize ? 2 : 4;
	}
	else if (size == 4 && Ofssize == USE16) {
		newflg = 3;
		shift = 2;
	}
	else {
		newflg = 1;
		shift = 1;
	}

	/* scan if there's a free register (pair/quadrupel) */
	for (firstreg = 0; firstreg < 4 && (newflg & *used); newflg <<= shift, firstreg += shift);
	if (firstreg >= 4) /* exit if nothing is free */
		return(0);

	paranode->sym.state = SYM_TMACRO;
	switch (size) {
	case 1:
		paranode->sym.regist[0] = watc_regs8[firstreg];
		break;
	case 2:
		paranode->sym.regist[0] = watc_regs16[firstreg];
		break;
	case 4:
		if (Ofssize) {
			paranode->sym.regist[0] = watc_regs32[firstreg];
		}
		else {
			paranode->sym.regist[0] = watc_regs16[firstreg];
			paranode->sym.regist[1] = watc_regs16[firstreg + 1];
		}
		break;
	case 8:
		if (Ofssize) {
			paranode->sym.regist[0] = watc_regs32[firstreg];
			paranode->sym.regist[1] = watc_regs32[firstreg + 1];
		}
		else {
			/* the AX:BX:CX:DX sequence is for 16-bit only.
			* fixme: no support for codeview debug info yet;
			* the S_REGISTER record supports max 2 registers only.
			*/
			for (firstreg = 0, regname[0] = NULLC; firstreg < 4; firstreg++) {
				GetResWName(watc_regs_qw[firstreg], regname + strlen(regname));
				if (firstreg != 3)
					strcat(regname, "::");
			}
		}
	}
	if (paranode->sym.regist[1]) {
		sprintf(regname, "%s::%s",
			GetResWName(paranode->sym.regist[1], regist),
			GetResWName(paranode->sym.regist[0], NULL));
	}
	else if (paranode->sym.regist[0]) {
		GetResWName(paranode->sym.regist[0], regname);
	}
	*used |= newflg;
	paranode->sym.string_ptr = LclAlloc(strlen(regname) + 1);
	strcpy(paranode->sym.string_ptr, regname);
	DebugMsg(("watc_pcheck(%s.%s): size=%u ptr=%u far=%u reg=%s\n", proc->sym.name, paranode->sym.name, size, paranode->sym.is_ptr, paranode->sym.isfar, regname));
	return(1);
}

static void watc_return(struct dsym *proc, char *buffer)
/********************************************************/
{
	int value;
	value = 4 * CurrWordSize;
	if (proc->e.procinfo->has_vararg == FALSE && proc->e.procinfo->parasize > value)
		sprintf(buffer + strlen(buffer), "%d%c", proc->e.procinfo->parasize - value, ModuleInfo.radix != 10 ? 't' : NULLC);
	return;
}
#endif

/* the MS Win32 fastcall ABI is simple: register ecx and edx are used,
* if the parameter's value fits into the register.
* there is no space reserved on the stack for a register backup.
* The 16-bit ABI uses registers AX, DX and BX - additional registers
* are pushed in PASCAL order (i.o.w.: left to right).
*/
static int ms32_pcheck(struct dsym *proc, struct dsym *paranode, int *used)
/***************************************************************************/
{
	char regname[32];
	int size = SizeFromMemtype(paranode->sym.mem_type, paranode->sym.Ofssize, paranode->sym.type);

	/* v2.07: 16-bit has 3 register params (AX,DX,BX) */
	//if ( size > CurrWordSize || *used >= 2 )
	if (size > CurrWordSize || *used >= ms32_maxreg[ModuleInfo.Ofssize] || paranode->sym.mem_type == MT_REAL4 || paranode->sym.mem_type == MT_REAL8)
		return(0);
	paranode->sym.state = SYM_TMACRO;
	/* v2.10: for codeview debug info, store the register index in the symbol */
	paranode->sym.regist[0] = ModuleInfo.Ofssize ? ms32_regs32[*used] : ms32_regs16[*used];
	GetResWName(ModuleInfo.Ofssize ? ms32_regs32[*used] : ms32_regs16[*used], regname);

	if (paranode->sym.mem_type == MT_WORD || paranode->sym.mem_type == MT_SWORD)
	{
		if (_stricmp(regname, "ECX") == 0)
			strcpy(regname, "cx");
		else if (_stricmp(regname, "EDX") == 0)
			strcpy(regname, "dx");
	}
	else if (paranode->sym.mem_type == MT_BYTE || paranode->sym.mem_type == MT_SBYTE)
	{
		if (_stricmp(regname, "ECX") == 0)
			strcpy(regname, "cl");
		else if (_stricmp(regname, "EDX") == 0)
			strcpy(regname, "dl");
	}

	paranode->sym.string_ptr = LclAlloc(strlen(regname) + 1);
	strcpy(paranode->sym.string_ptr, regname);
	(*used)++;
	return(1);
}

static void ms32_return(struct dsym *proc, char *buffer)
/********************************************************/
{
	/* v2.07: changed */
	//if( proc->e.procinfo->parasize > ( 2 * CurrWordSize ) )
	//    sprintf( buffer + strlen( buffer ), "%d%c", proc->e.procinfo->parasize - (2 * CurrWordSize), ModuleInfo.radix != 10 ? 't' : NULLC );
	if (proc->e.procinfo->parasize > (ms32_maxreg[ModuleInfo.Ofssize] * CurrWordSize))
		sprintf(buffer + strlen(buffer), "%d%c", proc->e.procinfo->parasize - (ms32_maxreg[ModuleInfo.Ofssize] * CurrWordSize), ModuleInfo.radix != 10 ? 't' : NULLC);
	return;
}

/* v2.29: delphi uses 3 register params (EAX,EDX,ECX) */
static int delphi_pcheck(struct dsym *proc, struct dsym *paranode, int *used)
/***************************************************************************/
{
	char regname[32];
	int size = SizeFromMemtype(paranode->sym.mem_type, paranode->sym.Ofssize, paranode->sym.type);
	int stack_size = size;

	if (paranode->sym.mem_type == MT_REAL4 || paranode->sym.mem_type == MT_REAL8)
	{
		if (stack_size < CurrWordSize) stack_size = CurrWordSize;
		proc->e.procinfo->ReservedStack += stack_size;
		return (0);
	}

	if (size > CurrWordSize || *used >= delphi_maxreg[ModuleInfo.Ofssize])
	{
		if (stack_size < CurrWordSize) stack_size = CurrWordSize;
		proc->e.procinfo->ReservedStack += stack_size;
		return(0);
	}

	paranode->sym.state = SYM_TMACRO;

	/* v2.29: for codeview debug info, store the register index in the symbol */
	GetResWName(delphi_regs32[*used], regname);

	if (paranode->sym.mem_type == MT_WORD || paranode->sym.mem_type == MT_SWORD)
	{
		if (_stricmp(regname, "EAX") == 0)
			strcpy(regname, "ax");
		else if (_stricmp(regname, "EDX") == 0)
			strcpy(regname, "dx");
		else if (_stricmp(regname, "ECX") == 0)
			strcpy(regname, "cx");
	}
	else if (paranode->sym.mem_type == MT_BYTE || paranode->sym.mem_type == MT_SBYTE)
	{
		if (_stricmp(regname, "EAX") == 0)
			strcpy(regname, "al");
		else if (_stricmp(regname, "EDX") == 0)
			strcpy(regname, "dl");
		else if (_stricmp(regname, "ECX") == 0)
			strcpy(regname, "cl");
	}

	paranode->sym.string_ptr = LclAlloc(strlen(regname) + 1);
	strcpy(paranode->sym.string_ptr, regname);
	(*used)++;
	return(1);
}

static void delphi_return(struct dsym *proc, char *buffer)
/********************************************************/
{
	if (proc->e.procinfo->parasize > (delphi_maxreg[ModuleInfo.Ofssize] * CurrWordSize))
		sprintf(buffer + strlen(buffer), "%d%c", proc->e.procinfo->parasize - (delphi_maxreg[ModuleInfo.Ofssize] * CurrWordSize), ModuleInfo.radix != 10 ? 't' : NULLC);
	return;
}

#if AMD64_SUPPORT

/* the MS Win64 fastcall ABI is strict: the first four parameters are
* passed in registers. If a parameter's value doesn't fit in a register,
* it's address is used instead. parameter 1 is stored in rcx/xmm0,
* then comes rdx/xmm1, r8/xmm2, r9/xmm3. The xmm regs are used if the
* param is a float/double (but not long double!).
* Additionally, there's space for the registers reserved by the caller on,
* the stack. On a function's entry it's located at [esp+8] for param 1,
* [esp+16] for param 2,... The parameter names refer to those stack
* locations, not to the register names.
*/
static int ms64_pcheck(struct dsym *proc, struct dsym *paranode, int *used)
/***************************************************************************/
{
	/* since the parameter names refer the stack-backup locations,
	* there's nothing to do here!
	* That is, if a parameter's size is > 8, it has to be changed
	* to a pointer. This is to be done yet.
	*/
	return(0);
}

static void ms64_return(struct dsym *proc, char *buffer)
/********************************************************/
{
	/* nothing to do, the caller cleans the stack */
	return;
}

#endif

static void pushitem(void *stk, void *elmt)
/*******************************************/
{
	void      **stack = stk;
	struct qnode *node;

	node = LclAlloc(sizeof(struct qnode));
	node->next = *stack;
	node->elmt = elmt;
	*stack = node;
}

static void *popitem(void *stk)
/*******************************/
{
	void        **stack = stk;
	struct qnode *node;
	void        *elmt;

	node = (struct qnode *)(*stack);
	*stack = node->next;
	elmt = (void *)node->elmt;
	LclFree(node);
	return(elmt);
}

static void push_proc(struct dsym *proc)
/****************************************/
{
	if (Parse_Pass == PASS_1) /* get the locals stored so far */
		SymGetLocal((struct asym *)proc);
	pushitem(&ProcStack, proc);
	return;
}

static struct dsym *pop_proc(void)
/**********************************/
{
	if (ProcStack == NULL)
		return(NULL);
	return((struct dsym *)popitem(&ProcStack));
}

/*
* LOCAL directive. Syntax:
* LOCAL symbol[,symbol]...
* symbol:name [[count]] [:[type]]
* count: number of array elements, default is 1
* type:  qualified type [simple type, structured type, ptr to simple/structured type]
*/
ret_code LocalDir(int i, struct asm_tok tokenarray[])
/*****************************************************/
{
	char        *name;
	struct dsym *local;
	struct dsym *curr;
	struct proc_info *info;
	struct qualified_type ti;

	if (Parse_Pass != PASS_1) /* everything is done in pass 1 */
		return(NOT_ERROR);

	DebugMsg1(("LocalDir(%u) entry\n", i));

	if (!(ProcStatus & PRST_PROLOGUE_NOT_DONE) || CurrProc == NULL) {
		return(EmitError(PROC_MACRO_MUST_PRECEDE_LOCAL));
	}

	info = CurrProc->e.procinfo;
#if STACKBASESUPP
	/* ensure the fpo bit is set - it's too late to set it in write_prologue().
	* Note that the fpo bit is set only IF there are locals or arguments.
	* fixme: what if pass > 1?
	*/
	if (GetRegNo(info->basereg) == 4) {
		info->fpo = TRUE;
		ProcStatus |= PRST_FPO;
	}
#endif

	i++; /* go past LOCAL */

	do {
		if (tokenarray[i].token != T_ID) {
			return(EmitErr(SYNTAX_ERROR_EX, tokenarray[i].string_ptr));
		}
		name = tokenarray[i].string_ptr;

		DebugMsg1(("LocalDir: item=%s\n", tokenarray[i].tokpos));

		ti.symtype = NULL;
		ti.is_ptr = 0;
		ti.ptr_memtype = MT_EMPTY;
		if (SIZE_DATAPTR & (1 << ModuleInfo.model))
			ti.is_far = TRUE;
		else
			ti.is_far = FALSE;
		ti.Ofssize = ModuleInfo.Ofssize;

#if 0
		/* since v1.95 a local hash table is used. No need to search the
		* symbol before SymLCreate() is called. SymLCreate() will display
		* an error if the symbol is already defined.
		*/
		if ((local = (struct dsym *)SymSearch(name)) && local->sym.state != SYM_UNDEFINED) {
			return(EmitErr(SYMBOL_ALREADY_DEFINED, name));
		}
#endif
		local = (struct dsym *)SymLCreate(name);
		if (!local) { /* if it failed, an error msg has been written already */
			DebugMsg(("LocalDir: SymLCreate( %s ) failed\n", name));
			return(ERROR);
		}
		if (ModuleInfo.win64_flags & W64F_SMART) local->sym.isparam = FALSE; //clear isparam var, added  by habran
		local->sym.state = SYM_STACK;
		local->sym.isdefined = TRUE;
		local->sym.total_length = 1; /* v2.04: added */
		switch (ti.Ofssize) {
		case USE16:
			local->sym.mem_type = MT_WORD;
			ti.size = sizeof(uint_16);
			break;
#if AMD64_SUPPORT
			/* v2.08: default type for locals in 64-bit is still DWORD (at least in Win64) */
			//case USE64: local->sym.mem_type = MT_QWORD; break;
			//ti.size = sizeof( uint_64 );
#endif
		default:
			local->sym.mem_type = MT_DWORD;
			ti.size = sizeof(uint_32);
			break;
		}

		i++; /* go past name */

			 /* get the optional index factor: local name[xx]:... */
		if (tokenarray[i].token == T_OP_SQ_BRACKET) {
			int j;
			struct expr opndx;
			i++; /* go past '[' */
				 /* scan for comma or colon. this isn't really necessary,
				 * but will prevent the expression evaluator from emitting
				 * confusing error messages.
				 */
			for (j = i; j < Token_Count; j++)
				if (tokenarray[j].token == T_COMMA ||
					tokenarray[j].token == T_COLON)
					break;
			if (ERROR == EvalOperand(&i, tokenarray, j, &opndx, 0))
				return(ERROR);
			if (opndx.kind != EXPR_CONST) {
				EmitError(CONSTANT_EXPECTED);
				opndx.value = 1;
			}
			/* zero is allowed as value! */
			local->sym.total_length = opndx.value;
			local->sym.isarray = TRUE;
			if (tokenarray[i].token == T_CL_SQ_BRACKET) {
				i++; /* go past ']' */
			}
			else {
				EmitError(EXPECTED_CL_SQ_BRACKET);
			}
		}

		/* get the optional type: local name[xx]:type  */
		if (tokenarray[i].token == T_COLON) {
			i++;

			if (GetQualifiedType(&i, tokenarray, &ti) == ERROR)
				return(ERROR);

			local->sym.mem_type = ti.mem_type;
			if (ti.mem_type == MT_TYPE) {
				local->sym.type = ti.symtype;
			}
			else {
				local->sym.target_type = ti.symtype;
			}
			DebugMsg1(("LocalDir: memtype=%X, type=%s, size=%u*%u\n",
				local->sym.mem_type,
				ti.symtype ? ti.symtype->name : "NULL",
				ti.size, local->sym.total_length));
		}
		local->sym.is_ptr = ti.is_ptr;
		local->sym.isfar = ti.is_far;
		local->sym.Ofssize = ti.Ofssize;
		local->sym.ptr_memtype = ti.ptr_memtype;
		local->sym.total_size = ti.size * local->sym.total_length;

		/* v2.12: address calculation is now done in SetLocalOffsets() */

		if (info->locallist == NULL) {
			info->locallist = local;
		}
		else {
			for (curr = info->locallist; curr->nextlocal; curr = curr->nextlocal);
			curr->nextlocal = local;
		}

		if (tokenarray[i].token != T_FINAL)
			if (tokenarray[i].token == T_COMMA) {
				if ((i + 1) < Token_Count)
					i++;
			}
			else {
				return(EmitErr(EXPECTING_COMMA, tokenarray[i].tokpos));
			}

	} while (i < Token_Count);

	return(NOT_ERROR);
}

#if STACKBASESUPP

/* read/write value of @StackBase variable */
void UpdateStackBase(struct asym *sym, struct expr *opnd)
/*********************************************************/
{
	if (opnd) {
		StackAdj = opnd->uvalue;
		StackAdjHigh = opnd->hvalue;
	}
	sym->value = StackAdj;
	sym->value3264 = StackAdjHigh;
}

/* read value of @ProcStatus variable */
void UpdateProcStatus(struct asym *sym, struct expr *opnd)
/**********************************************************/
{
	sym->value = (CurrProc ? ProcStatus : 0);
}

#endif

/* parse parameters of a PROC/PROTO.
* Called in pass one only.
* i=start parameters
*/
static ret_code ParseParams(struct dsym *proc, int i, struct asm_tok tokenarray[], bool IsPROC)
/***********************************************************************************************/
{
	char            *name;
	struct asym     *sym;
	int             cntParam;
	int             offset = 0;
	int             fcint = 0;
	int             vecint = 0;
	struct qualified_type ti;
	bool            is_vararg;
	bool            init_done;
	struct dsym     *paranode;
	struct dsym     *paracurr;
	int             curr;

	/*
	* find "first" parameter ( that is, the first to be pushed in INVOKE ).
	*/
	if (proc->sym.langtype == LANG_C ||
		proc->sym.langtype == LANG_SYSCALL ||
		proc->sym.langtype == LANG_DELPHICALL ||
		(proc->sym.langtype == LANG_FASTCALL && ModuleInfo.Ofssize != USE64) ||
		(proc->sym.langtype == LANG_VECTORCALL && ModuleInfo.Ofssize != USE64) ||
		(proc->sym.langtype == LANG_SYSVCALL && ModuleInfo.Ofssize != USE64) ||
		proc->sym.langtype == LANG_STDCALL)
		for (paracurr = proc->e.procinfo->paralist; paracurr && paracurr->nextparam; paracurr = paracurr->nextparam);
	else
		paracurr = proc->e.procinfo->paralist;

	/* v2.11: proc_info.init_done has been removed, sym.isproc flag is used instead */
	init_done = proc->sym.isproc;

	for (cntParam = 0; tokenarray[i].token != T_FINAL; cntParam++) {
		if (tokenarray[i].token == T_ID) {
			name = tokenarray[i++].string_ptr;
		}
		else if (IsPROC == FALSE && tokenarray[i].token == T_COLON) {
			if (paracurr)
				name = paracurr->sym.name;
			else
				name = "";
		}
		else {

			/* PROC needs a parameter name, PROTO accepts <void> also */
			DebugMsg(("ParseParams: name missing/invalid for parameter %u, i=%u\n", cntParam + 1, i));
			return(EmitErr(SYNTAX_ERROR_EX, tokenarray[i].string_ptr));
		}

		ti.symtype = NULL;
		ti.is_ptr = 0;
		ti.ptr_memtype = MT_EMPTY;
		/* v2.02: init is_far depending on memory model */
		//ti.is_far = FALSE;
		if (SIZE_DATAPTR & (1 << ModuleInfo.model))
			ti.is_far = TRUE;
		else
			ti.is_far = FALSE;
		ti.Ofssize = ModuleInfo.Ofssize;
		ti.size = CurrWordSize;

		is_vararg = FALSE;

		/* read colon. It's optional for PROC.
		* Masm also allows a missing colon for PROTO - if there's
		* just one parameter. Probably a Masm bug.
		* Uasm always require a colon for PROTO.
		*/
		if (tokenarray[i].token != T_COLON) {
			if (IsPROC == FALSE) {
				return(EmitError(COLON_EXPECTED));
			}
			switch (ti.Ofssize) {
			case USE16:
				ti.mem_type = MT_WORD; break;
#if AMD64_SUPPORT
				/* v2.08: default size for arguments is DWORD in 64-bit ( Win64 ) */
				//case USE64: ti.mem_type = MT_QWORD; break;
#endif
			default:
				ti.mem_type = MT_DWORD; break;
			}
		}
		else {
			i++;
			if ((tokenarray[i].token == T_RES_ID) && (tokenarray[i].tokval == T_VARARG)) {
				switch (proc->sym.langtype) {
				case LANG_NONE:
				case LANG_BASIC:
				case LANG_FORTRAN:
				case LANG_PASCAL:
				case LANG_STDCALL:
					return(EmitError(VARARG_REQUIRES_C_CALLING_CONVENTION));
				}
				/* v2.05: added check */
				if (tokenarray[i + 1].token != T_FINAL)
					EmitError(VARARG_PARAMETER_MUST_BE_LAST);
				else
					is_vararg = TRUE;
				ti.mem_type = MT_EMPTY;
				ti.size = 0;
				i++;
			}
			else {
				if (GetQualifiedType(&i, tokenarray, &ti) == ERROR)
					return(ERROR);
			}
		}

		/* check if parameter name is defined already */
		if ((IsPROC) && (sym = SymSearch(name)) && sym->state != SYM_UNDEFINED) { 
			DebugMsg(("ParseParams: %s defined already, state=%u, local=%u\n", sym->name, sym->state, sym->scoped));
			return(EmitErr(SYMBOL_REDEFINITION, name));
		}

		/* redefinition? */
		if (paracurr) {
			struct asym *to;
			struct asym *tn;
			char oo;
			char on;
			for (tn = ti.symtype; tn && tn->type; tn = tn->type);
			/* v2.12: don't assume pointer type if mem_type is != MT_TYPE!
			* regression test proc9.asm.
			*/
			//to = ( paracurr->sym.mem_type == MT_TYPE ) ? paracurr->sym.type : paracurr->sym.target_type;
			if (paracurr->sym.mem_type == MT_TYPE)
				to = paracurr->sym.type;
			else
				to = (paracurr->sym.mem_type == MT_PTR ? paracurr->sym.target_type : NULL);
			for (; to && to->type; to = to->type);
			oo = (paracurr->sym.Ofssize != USE_EMPTY) ? paracurr->sym.Ofssize : ModuleInfo.Ofssize;
			on = (ti.Ofssize != USE_EMPTY) ? ti.Ofssize : ModuleInfo.Ofssize;
			if (ti.mem_type != paracurr->sym.mem_type ||
				(ti.mem_type == MT_TYPE && tn != to) ||
				(ti.mem_type == MT_PTR &&
				(ti.is_far != paracurr->sym.isfar ||
					on != oo ||
					ti.ptr_memtype != paracurr->sym.ptr_memtype ||
					tn != to))) {

				/* UASM 2.46.10 prevent symbols that are moved to stack whose size is turned from ptr to machine word size from breaking the proto vs proc defition of a ptr type */
				/* UASM 2.47.1 added additional types */
				if (ti.mem_type == MT_PTR && paracurr->sym.state == SYM_STACK && 
					(paracurr->sym.mem_type == MT_QWORD && CurrWordSize == 8) ||
					(paracurr->sym.mem_type == MT_OWORD && CurrWordSize == 8) ||
					(paracurr->sym.mem_type == MT_YMMWORD && CurrWordSize == 8) ||
					(paracurr->sym.mem_type == MT_ZMMWORD && CurrWordSize == 8) ||
					(paracurr->sym.mem_type == MT_DWORD && CurrWordSize == 4) ||
					(paracurr->sym.mem_type == MT_OWORD && CurrWordSize == 4) ||
					(paracurr->sym.mem_type == MT_YMMWORD && CurrWordSize == 4) ||
					(paracurr->sym.mem_type == MT_ZMMWORD && CurrWordSize == 4))
				{

				}
				else if (paracurr->sym.mem_type == MT_PTR && paracurr->sym.state == SYM_STACK &&
					(ti.mem_type == MT_QWORD && CurrWordSize == 8) ||
					(ti.mem_type == MT_OWORD && CurrWordSize == 8) ||
					(ti.mem_type == MT_YMMWORD && CurrWordSize == 8) ||
					(ti.mem_type == MT_ZMMWORD && CurrWordSize == 8) ||
					(ti.mem_type == MT_DWORD && CurrWordSize == 4) ||
					(ti.mem_type == MT_OWORD && CurrWordSize == 4) ||
					(ti.mem_type == MT_YMMWORD && CurrWordSize == 4) ||
					(ti.mem_type == MT_ZMMWORD && CurrWordSize == 4))
				{

				}
				else
				{
					DebugMsg(("ParseParams: old-new memtype=%X-%X type=%X(%s)-%X(%s) far=%u-%u ind=%u-%u ofss=%d-%d pmt=%X-%X\n",
						paracurr->sym.mem_type, ti.mem_type,
						(paracurr->sym.mem_type == MT_TYPE) ? paracurr->sym.type : paracurr->sym.target_type,
						(paracurr->sym.mem_type == MT_TYPE) ? paracurr->sym.type->name : paracurr->sym.target_type ? paracurr->sym.target_type->name : "",
						ti.symtype, ti.symtype ? ti.symtype->name : "",
						paracurr->sym.isfar, ti.is_far,
						paracurr->sym.is_ptr, ti.is_ptr,
						paracurr->sym.Ofssize, ti.Ofssize,
						paracurr->sym.ptr_memtype, ti.ptr_memtype));
					EmitErr(CONFLICTING_PARAMETER_DEFINITION, name);
				}
			}

			if (IsPROC) {
				DebugMsg1(("ParseParams: calling SymAddLocal(%s, %s)\n", paracurr->sym.name, name));
				/* it has been checked already that the name isn't found - SymAddLocal() shouldn't fail */
				SymAddLocal(&paracurr->sym, name);
			}
			/* set paracurr to next parameter */
			if (proc->sym.langtype == LANG_C ||
				proc->sym.langtype == LANG_SYSCALL ||
				proc->sym.langtype == LANG_DELPHICALL ||
				(proc->sym.langtype == LANG_FASTCALL && ti.Ofssize != USE64) ||
				(proc->sym.langtype == LANG_VECTORCALL && ti.Ofssize != USE64) ||
				(proc->sym.langtype == LANG_SYSVCALL && ti.Ofssize != USE64) ||
				proc->sym.langtype == LANG_STDCALL) {
				struct dsym *l;
				for (l = proc->e.procinfo->paralist;
					l && (l->nextparam != paracurr);
					l = l->nextparam);
				paracurr = l;
			}
			else
				paracurr = paracurr->nextparam;
		}
		else if (init_done == TRUE) {
			/* second definition has more parameters than first */
			DebugMsg(("ParseParams: different param count\n"));
			return(EmitErr(CONFLICTING_PARAMETER_DEFINITION, ""));
		}
		else {
			if (IsPROC) {
				paranode = (struct dsym *)SymLCreate(name);
			}
			else
				paranode = (struct dsym *)SymAlloc("");/* for PROTO, no param name needed */

			if (paranode == NULL) { /* error msg has been displayed already */
				DebugMsg(("ParseParams: SymLCreate(%s) failed\n", name));
				return(ERROR);
			}
			paranode->sym.isdefined = TRUE;
			paranode->sym.mem_type = ti.mem_type;
			if (ti.mem_type == MT_TYPE) {
				paranode->sym.type = ti.symtype;
				/* this is where vectors are intercepted  and writen to the proc */
				if (proc->sym.langtype == LANG_VECTORCALL) {
					proc->e.procinfo->vecregsize[cntParam] = ti.symtype->max_mbr_size;
					proc->e.procinfo->vecregs[cntParam] = ti.size / ti.symtype->max_mbr_size;
					proc->e.procinfo->vsize += ti.size;
					ti.size = MT_QWORD;
				}
			}
			else {
				paranode->sym.target_type = ti.symtype;
				/* this is where vectors are intercepted  and writen to the proc */
				if (proc->sym.langtype == LANG_VECTORCALL) {
					if (ti.mem_type == MT_REAL4 || ti.mem_type == MT_REAL8 ||
						ti.mem_type == MT_OWORD || ti.mem_type == MT_YMMWORD || ti.mem_type == MT_ZMMWORD) {
						proc->e.procinfo->vecregsize[cntParam] = ti.size;
						proc->e.procinfo->vecregs[cntParam] = 1;
						if (ti.size >= 16) proc->e.procinfo->vsize += ti.size;
						ti.size = MT_QWORD;
					}
				}
			}

			/* v2.05: moved BEFORE fastcall_tab() */
			paranode->sym.isfar = ti.is_far;
			paranode->sym.Ofssize = ti.Ofssize;
			paranode->sym.is_ptr = ti.is_ptr;
			paranode->sym.ptr_memtype = ti.ptr_memtype;
			paranode->sym.is_vararg = is_vararg;
			if (proc->sym.langtype == LANG_FASTCALL && fastcall_tab[ModuleInfo.fctype].paramcheck(proc, paranode, &fcint))
			{
			}
			else if (proc->sym.langtype == LANG_VECTORCALL && vectorcall_tab[ModuleInfo.fctype].paramcheck(proc, paranode, &fcint))
			{
			}
			else if (proc->sym.langtype == LANG_SYSVCALL && sysvcall_tab[ModuleInfo.fctype].paramcheck(proc, paranode, &fcint, &vecint))
			{
			}
			else if (proc->sym.langtype == LANG_DELPHICALL && delphicall_tab[ModuleInfo.fctype].paramcheck(proc, paranode, &fcint))
			{
			}
			else
			{
				paranode->sym.state = SYM_STACK;
			}

			paranode->sym.total_length = 1; /* v2.04: added */
			paranode->sym.total_size = ti.size;

			if (paranode->sym.is_vararg == FALSE)
			{
				if (proc->sym.langtype == LANG_VECTORCALL)
				{
					switch (CurrWordSize)
					{
					case 8:
						switch (ti.mem_type)
						{
						case MT_OWORD:
							proc->e.procinfo->parasize += ROUND_UP(ti.size, IsPROC ? 2 * CurrWordSize : 2 * (2 << proc->sym.seg_ofssize));
							break;

						case MT_YMMWORD:
							proc->e.procinfo->parasize += ROUND_UP(ti.size, IsPROC ? 4 * CurrWordSize : 4 * (2 << proc->sym.seg_ofssize));
							break;

						case MT_ZMMWORD:
							proc->e.procinfo->parasize += ROUND_UP(ti.size, IsPROC ? 8 * CurrWordSize : 8 * (2 << proc->sym.seg_ofssize));
							break;

						default:
							proc->e.procinfo->parasize += ROUND_UP(ti.size, IsPROC ? CurrWordSize : (2 << proc->sym.seg_ofssize));
							break;
						}
						break;

					case 4:
						switch (ti.mem_type)
						{
						case MT_OWORD:
							proc->e.procinfo->parasize += ROUND_UP(ti.size, IsPROC ? 4 * CurrWordSize : 4 * (2 << proc->sym.seg_ofssize));
							break;

						case MT_YMMWORD:
							proc->e.procinfo->parasize += ROUND_UP(ti.size, IsPROC ? 8 * CurrWordSize : 8 * (2 << proc->sym.seg_ofssize));
							break;

						case MT_ZMMWORD:
							proc->e.procinfo->parasize += ROUND_UP(ti.size, IsPROC ? 16 * CurrWordSize : 16 * (2 << proc->sym.seg_ofssize));
							break;

						default:
							proc->e.procinfo->parasize += ROUND_UP(ti.size, IsPROC ? CurrWordSize : (2 << proc->sym.seg_ofssize));
							break;
						}
						break;

					default:
						proc->e.procinfo->parasize += ROUND_UP(ti.size, IsPROC ? CurrWordSize : (2 << proc->sym.seg_ofssize));
						break;
					}
				}
				else
				{
					proc->e.procinfo->parasize += ROUND_UP(ti.size, IsPROC ? CurrWordSize : (2 << proc->sym.seg_ofssize));
				}
			}

			/* v2.05: the PROC's vararg flag has been set already */
			//proc->e.procinfo->is_vararg |= paranode->sym.is_vararg;

			/* Parameters usually are stored in "push" order.
			* However, for Win64, it's better to store them
			* the "natural" way from left to right, since the
			* arguments aren't "pushed".
			*/

			switch (proc->sym.langtype) {
			case LANG_BASIC:
			case LANG_FORTRAN:
			case LANG_PASCAL:
			left_to_right:
				paranode->nextparam = NULL;
				if (proc->e.procinfo->paralist == NULL) {
					proc->e.procinfo->paralist = paranode;
				}
				else {
					for (paracurr = proc->e.procinfo->paralist;; paracurr = paracurr->nextparam) {
						if (paracurr->nextparam == NULL) {
							break;
						}
					}
					paracurr->nextparam = paranode;
					paracurr = NULL;
				}
				break;
				//#if AMD64_SUPPORT
				//case LANG_SYSVCALL:
				//paranode->nextparam = proc->e.procinfo->paralist;
				// proc->e.procinfo->paralist = paranode;
				//break;
				// #endif
			case LANG_FASTCALL:
			case LANG_VECTORCALL:
			case LANG_DELPHICALL:
#if AMD64_SUPPORT
			case LANG_SYSVCALL:
				if (ti.Ofssize == USE64)
					goto left_to_right;
#endif
				/* v2.07: MS fastcall 16-bit is PASCAL! */
				if (ti.Ofssize == USE16 && ModuleInfo.fctype == FCT_MSC)
					goto left_to_right;
				else if (ti.Ofssize == USE32 && ModuleInfo.fctype == FCT_DELPHI && proc->sym.langtype == LANG_DELPHICALL)
					goto left_to_right;
			default:
				paranode->nextparam = proc->e.procinfo->paralist;
				proc->e.procinfo->paralist = paranode;
				break;
			}
		}
		if (tokenarray[i].token != T_FINAL) {
			if (tokenarray[i].token != T_COMMA) {
				DebugMsg(("ParseParams: error, cntParam=%u, found %s\n", cntParam, tokenarray[i].tokpos));
				return(EmitErr(EXPECTING_COMMA, tokenarray[i].tokpos));
			}
			i++;    /* go past comma */
		}
	} /* end for */
	  //if (proc->sym.langtype == LANG_VECTORCALL)__debugbreak();
	  //if ( proc->e.procinfo->init_done == TRUE ) {
	if (init_done == TRUE) {
		if (paracurr) {
			/* first definition has more parameters than second */
			DebugMsg(("ParseParams: a param is left over, cntParam=%u\n", cntParam));
			return(EmitErr(CONFLICTING_PARAMETER_DEFINITION, ""));
		}
	}

	if (IsPROC) {
		/* calc starting offset for parameters,
		* offset from [E|R]BP : return addr + old [E|R]BP
		* NEAR: 2 * wordsize, FAR: 3 * wordsize
		*         NEAR  FAR
		*-------------------------
		* USE16   +4    +6
		* USE32   +8    +12
		* USE64   +16   +24
		* without frame pointer:
		* USE16   +2    +4
		* USE32   +4    +8
		* USE64   +8    +16
		*/
		if (proc->e.procinfo->fpo || (proc->e.procinfo->parasize == 0 && proc->e.procinfo->locallist == NULL) && proc->e.procinfo->basereg == T_RSP)
			offset = ((2 + (proc->sym.mem_type == MT_FAR ? 1 : 0)) * CurrWordSize);
		// Compensate for the stack-frame setup of RBP including the push rbp, which moves the parameters out by 8.
		else if (proc->e.procinfo->basereg == T_RBP && (ModuleInfo.win64_flags & W64F_AUTOSTACKSP) && (ModuleInfo.win64_flags & W64F_SAVEREGPARAMS))
		{
			offset = ((2 + (proc->sym.mem_type == MT_FAR ? 1 : 0)) * CurrWordSize);
		}
		else if (proc->e.procinfo->basereg == T_RBP && !(ModuleInfo.win64_flags & W64F_AUTOSTACKSP) && (ModuleInfo.win64_flags & W64F_SAVEREGPARAMS))
		{
			offset = ((2 + (proc->sym.mem_type == MT_FAR ? 1 : 0)) * CurrWordSize);
		}
		else if (proc->e.procinfo->basereg == T_RBP)
			offset = ((2 + (proc->sym.mem_type == MT_FAR ? 1 : 0)) * CurrWordSize);
		else
			offset = ((2 + (proc->sym.mem_type == MT_FAR ? 1 : 0)) * CurrWordSize);

		/* now calculate the [E|R]BP offsets */

#if AMD64_SUPPORT
		if (ModuleInfo.Ofssize == USE64) {
			if (proc->sym.langtype == LANG_FASTCALL || proc->sym.langtype == LANG_VECTORCALL || proc->sym.langtype == LANG_SYSVCALL)
			{
				for (paranode = proc->e.procinfo->paralist; paranode; paranode = paranode->nextparam)
					if (paranode->sym.state == SYM_TMACRO) /* register param */
						;
					else {
						paranode->sym.offset = offset;
						proc->e.procinfo->stackparam = TRUE;
						offset += ROUND_UP(paranode->sym.total_size, CurrWordSize);
						/* set isparam var for W64F_SMART */
						//if (ModuleInfo.win64_flags & W64F_SMART) 
						if(ModuleInfo.basereg[ModuleInfo.Ofssize] == T_RSP)
							paranode->sym.isparam = TRUE;
					}
			}
		}
		else
#endif
			for (; cntParam; cntParam--)
			{
				for (curr = 1, paranode = proc->e.procinfo->paralist; curr < cntParam; paranode = paranode->nextparam, curr++);
				DebugMsg1(("ParseParams: parm=%s, ofs=%u, size=%d\n", paranode->sym.name, offset, paranode->sym.total_size));
				if (paranode->sym.state == SYM_TMACRO) /* register param? */
					;
				else
				{
					paranode->sym.offset = offset;
					proc->e.procinfo->stackparam = TRUE;
					offset += ROUND_UP(paranode->sym.total_size, CurrWordSize);
				}
			}
	}
	return (NOT_ERROR);
}

/*
* parse a function prototype - called in pass 1 only.
* the syntax is used by:
* - PROC directive:      <name> PROC ...
* - PROTO directive:     <name> PROTO ...
* - EXTERN[DEF] directive: EXTERN[DEF] <name>: PROTO ...
* - TYPEDEF directive:   <name> TYPEDEF PROTO ...
*
* i = start index of attributes
* IsPROC: TRUE for PROCs, FALSE for everything else
*
* strategy to set default value for "offset size" (16/32):
* 1. if current model is FLAT, use 32, else
* 2. use the current segment's attribute
* 3. if no segment is set, use cpu setting
*/
ret_code ParseProc(struct dsym *proc, int i, struct asm_tok tokenarray[], bool IsPROC, enum lang_type langtype)
/***************************************************************************************************************/
{
	char            *token;
	uint_16         *regist;
	enum memtype    newmemtype;
	uint_8          newofssize;
	uint_8          oldofssize;
#if FASTPASS
	bool            oldpublic = proc->sym.ispublic;
#endif
	enum returntype ret_type;
	bool defRet = FALSE;
	struct asym *sym = NULL;

	/* set some default values */

	if (IsPROC) {
		proc->e.procinfo->isexport = ModuleInfo.procs_export;
		/* don't overwrite a PUBLIC directive for this symbol! */
		if (ModuleInfo.procs_private == FALSE)
			proc->sym.ispublic = TRUE;

		/* set type of epilog code */
#if STACKBASESUPP
		/* v2.11: if base register isn't [E|R]BP, don't use LEAVE! */
		if (GetRegNo(proc->e.procinfo->basereg) != 5) {
			proc->e.procinfo->pe_type = 0;
		}
		else
#endif
			if (Options.masm_compat_gencode) {
				/* v2.07: Masm uses LEAVE if
				* - current code is 32-bit/64-bit or
				* - cpu is .286 or .586+ */
				//proc->e.procinfo->pe_type = ( ( ModuleInfo.curr_cpu & P_CPU_MASK ) >= P_286 );
				proc->e.procinfo->pe_type = (ModuleInfo.Ofssize > USE16 ||
					(ModuleInfo.curr_cpu & P_CPU_MASK) == P_286 ||
					(ModuleInfo.curr_cpu & P_CPU_MASK) >= P_586) ? 1 : 0;
			}
			else {
				/* use LEAVE for 286, 386 (and x64) */
				proc->e.procinfo->pe_type = ((ModuleInfo.curr_cpu & P_CPU_MASK) == P_286 ||
#if AMD64_SUPPORT
				(ModuleInfo.curr_cpu & P_CPU_MASK) == P_64 ||
#endif
					(ModuleInfo.curr_cpu & P_CPU_MASK) == P_386) ? 1 : 0;
			}
	}

#if MANGLERSUPP
	/* OW name mangling */
	if (tokenarray[i].token == T_STRING && IsPROC) {
		/* SetMangler() will ignore LANG_NONE */
		SetMangler(&proc->sym, LANG_NONE, tokenarray[i].string_ptr);
		i++;
	}
#endif

	/* 1. attribute is <distance> */
	if (tokenarray[i].token == T_STYPE &&
		tokenarray[i].tokval >= T_NEAR && tokenarray[i].tokval <= T_FAR32) {
		uint_8 Ofssize = GetSflagsSp(tokenarray[i].tokval);
		/* v2.06: SimpleType is obsolete */
		/* v2.05: FindStdType() is obsolete */
		//type = tokenarray[i].bytval;
		//type = FindStdType(tokenarray[i].value);
		if (IsPROC) {
			if ((ModuleInfo.Ofssize >= USE32 && Ofssize == USE16) ||
				(ModuleInfo.Ofssize == USE16 && Ofssize == USE32)) {
				EmitError(DISTANCE_INVALID);
			}
		}
		newmemtype = GetMemtypeSp(tokenarray[i].tokval);
		newofssize = ((Ofssize != USE_EMPTY) ? Ofssize : ModuleInfo.Ofssize);
		i++;
	}
	else {
		newmemtype = ((SIZE_CODEPTR & (1 << ModuleInfo.model)) ? MT_FAR : MT_NEAR);
		newofssize = ModuleInfo.Ofssize;
	}

	/* v2.11: GetSymOfssize() cannot handle SYM_TYPE correctly */
	if (proc->sym.state == SYM_TYPE)
		oldofssize = proc->sym.seg_ofssize;
	else
		oldofssize = GetSymOfssize(&proc->sym);

	/* did the distance attribute change? */
	if (proc->sym.mem_type != MT_EMPTY &&
		(proc->sym.mem_type != newmemtype ||
			oldofssize != newofssize)) {
		DebugMsg(("ParseProc: error, memtype changed, old-new memtype=%X-%X, ofssize=%X-%X\n", proc->sym.mem_type, newmemtype, proc->sym.Ofssize, newofssize));
		if (proc->sym.mem_type == MT_NEAR || proc->sym.mem_type == MT_FAR)
			EmitError(PROC_AND_PROTO_CALLING_CONV_CONFLICT);
		else {
			return(EmitErr(SYMBOL_REDEFINITION, proc->sym.name));
		}
	}
	else {
		proc->sym.mem_type = newmemtype;
		if (IsPROC == FALSE)
			proc->sym.seg_ofssize = newofssize;
	}

	/* 2. attribute is <langtype> */
	/* v2.09: the default language value is now a function argument. This is because
	* EXTERN[DEF] allows to set the language attribute by:
	* EXTERN[DEF] <langtype> <name> PROTO ...
	* ( see CreateProto() in extern.c )
	*/
	langtype = ModuleInfo.langtype; /* set the default value */
	GetLangType(&i, tokenarray, &langtype); /* optionally overwrite the value */

											/* has language changed? */
	if (proc->sym.langtype != LANG_NONE && proc->sym.langtype != langtype) {
		DebugMsg(("ParseProc: error, language changed, %u - %u\n", proc->sym.langtype, langtype));
		EmitError(PROC_AND_PROTO_CALLING_CONV_CONFLICT);
	}
	else
		proc->sym.langtype = langtype;


	/* Handle return type if present */
	ret_type = 0xff;
	if (proc->e.procinfo->ret_type == 0xff)
	{
		if (ModuleInfo.Ofssize == USE16)
			proc->e.procinfo->ret_type = RT_WORD;
		if (ModuleInfo.Ofssize == USE32)
			proc->e.procinfo->ret_type = RT_DWORD;
		if (ModuleInfo.Ofssize == USE64)
			proc->e.procinfo->ret_type = RT_QWORD;
		defRet = TRUE;
	}

	/* UASM 2.46.7 set leaf tracking */
	proc->e.procinfo->isleaf = TRUE;

	/* Could be a typedef/chain of typedefs terminating in a valid basic type UASM 2.46.8 */
	/* UASM 2.46.9 put return type in () */

	if (tokenarray[i + 1].tokval == T_VOIDARG)
	{
		i += 3;
	}
	else if (tokenarray[i].token == T_OP_BRACKET && tokenarray[i+2].token == T_CL_BRACKET && tokenarray[i+1].token == T_ID )
	{
		sym = SymLookup(tokenarray[i + 1].string_ptr);
		while (sym)
		{
			switch (sym->mem_type)
			{
			case MT_EMPTY:
				/* UASM 2.46.10 - Could be a vectorcall type return */
				if (sym->state == SYM_TYPE)
				{
					if (sym->total_size == 16)
						ret_type = RT_XMM;
					else if (sym->total_size == 32)
						ret_type = RT_YMM;
					else if (sym->total_size == 64)
						ret_type = RT_ZMM;
				}
				break;
			case MT_BYTE:
				ret_type = RT_BYTE;
				break;
			case MT_SBYTE:
				ret_type = RT_SBYTE;
				break;
			case MT_WORD:
				ret_type = RT_WORD;
				break;
			case MT_SWORD:
				ret_type = RT_SWORD;
				break;
			case MT_DWORD:
				ret_type = RT_DWORD;
				break;
			case MT_SDWORD:
				ret_type = RT_SDWORD;
				break;
			case MT_QWORD:
				ret_type = RT_QWORD;
				break;
			case MT_SQWORD:
				ret_type = RT_SQWORD;
				break;
			case MT_FLOAT:
				ret_type = RT_FLOAT;
				break;
			case MT_OWORD:
				ret_type = RT_XMM;
				break;
			case MT_PTR:
				ret_type = RT_PTR;
				break;
			case MT_YMMWORD:
				ret_type = RT_YMM;
				break;
			case MT_ZMMWORD:
				ret_type = RT_ZMM;
				break;
			case MT_REAL4:
				ret_type = RT_REAL4;
				break;
			case MT_REAL8:
				ret_type = RT_REAL8;
				break;
			case MT_REAL10:
				ret_type = RT_REAL10;
				break;
			}
			if (sym->target_type && sym->mem_type != MT_EMPTY)
				sym = sym->target_type;
			else
				break;
		}
		i+=3;
	}
	else if (tokenarray[i].token == T_OP_BRACKET && tokenarray[i + 2].token == T_CL_BRACKET && 
		     (tokenarray[i+1].token == T_STYPE || (tokenarray[i+1].token == T_BINARY_OPERATOR && tokenarray[i+1].tokval == T_PTR)) )
	{
		switch (tokenarray[i+1].tokval)
		{
		case T_PTR:
			ret_type = RT_PTR;
			break;
		case T_REAL4:
			ret_type = RT_REAL4;
			break;
		case T_REAL8:
			ret_type = RT_REAL8;
			break;
		case T_BYTE:
			ret_type = RT_BYTE;
			break;
		case T_WORD:
			ret_type = RT_WORD;
			break;
		case T_DWORD:
			ret_type = RT_DWORD;
			break;
		case T_QWORD:
			ret_type = RT_QWORD;
			break;
		case T_SBYTE:
			ret_type = RT_SBYTE;
			break;
		case T_SWORD:
			ret_type = RT_SWORD;
			break;
		case T_SDWORD:
			ret_type = RT_SDWORD;
			break;
		case T_SQWORD:
			ret_type = RT_SQWORD;
			break;
		case T_XMMWORD:
			ret_type = RT_XMM;
			break;
		case T_YMMWORD:
			ret_type = RT_YMM;
			break;
		case T_ZMMWORD:
			ret_type = RT_ZMM;
			break;
		default:
			ret_type = RT_NONE;
			break;
		}

		i+=3;
	}
	else
	{
		ret_type = proc->e.procinfo->ret_type; /* wasn't specified on proc, assume settings from proto */
	}

	if (proc->e.procinfo->ret_type != 0xff && !defRet)
	{
		if (ret_type != proc->e.procinfo->ret_type)
			EmitError(PROC_AND_PROTO_CALLING_CONV_CONFLICT);
	}
	proc->e.procinfo->ret_type = ret_type;

	/* 3. attribute is <visibility> */
	/* note that reserved word PUBLIC is a directive! */
	/* PROTO does NOT accept PUBLIC! However,
	* PROTO accepts PRIVATE and EXPORT, but these attributes are just ignored!
	*/

	if (tokenarray[i].token == T_ID || tokenarray[i].token == T_DIRECTIVE) {
		token = tokenarray[i].string_ptr;
		if (_stricmp(token, "PRIVATE") == 0) {
			if (IsPROC) { /* v2.11: ignore PRIVATE for PROTO */
				proc->sym.ispublic = FALSE;
#if FASTPASS
				/* error if there was a PUBLIC directive! */
				proc->sym.scoped = TRUE;
				if (oldpublic) {
					SkipSavedState(); /* do a full pass-2 scan */
				}
#endif
				proc->e.procinfo->isexport = FALSE;
			}
			i++;
		}
		else if (IsPROC && (_stricmp(token, "PUBLIC") == 0)) {
			proc->sym.ispublic = TRUE;
			proc->e.procinfo->isexport = FALSE;
			i++;
		}
		else if (_stricmp(token, "EXPORT") == 0) {
			DebugMsg1(("ParseProc(%s): EXPORT detected\n", proc->sym.name));
			if (IsPROC) { /* v2.11: ignore EXPORT for PROTO */
				proc->sym.ispublic = TRUE;
				proc->e.procinfo->isexport = TRUE;
				/* v2.11: no export for 16-bit near */
				if (ModuleInfo.Ofssize == USE16 && proc->sym.mem_type == MT_NEAR)
					EmitErr(EXPORT_MUST_BE_FAR, proc->sym.name);
			}
			i++;
		}
	}

	/* 4. attribute is <prologuearg>, for PROC only.
	* it must be enclosed in <>
	*/
	if (IsPROC && tokenarray[i].token == T_STRING && tokenarray[i].string_delim == '<') {
		int idx = Token_Count + 1;
		int max;
		if (ModuleInfo.prologuemode == PEM_NONE)
			; /* no prologue at all */
		else if (ModuleInfo.prologuemode == PEM_MACRO) {
			proc->e.procinfo->prologuearg = LclAlloc(tokenarray[i].stringlen + 1);
			strcpy(proc->e.procinfo->prologuearg, tokenarray[i].string_ptr);
		}
		else {
			/* check the argument. The default prologue
			understands FORCEFRAME and LOADDS only
			*/
			max = Tokenize(tokenarray[i].string_ptr, idx, tokenarray, TOK_RESCAN);
			for (; idx < max; idx++) {
				if (tokenarray[idx].token == T_ID) {
					if (_stricmp(tokenarray[idx].string_ptr, "FORCEFRAME") == 0) {
						proc->e.procinfo->forceframe = TRUE;
#if AMD64_SUPPORT
					}
					else if (ModuleInfo.Ofssize != USE64 && (_stricmp(tokenarray[idx].string_ptr, "LOADDS") == 0)) {
#else
					}
					else if (_stricmp(tokenarray[idx].string_ptr, "LOADDS") == 0) {
#endif
						if (ModuleInfo.model == MODEL_FLAT) {
							EmitWarn(2, LOADDS_IGNORED_IN_FLAT_MODEL);
						}
						else
							proc->e.procinfo->loadds = TRUE;
					}
					else {
						return(EmitErr(UNKNOWN_DEFAULT_PROLOGUE_ARGUMENT, tokenarray[idx].string_ptr));
					}
					if (tokenarray[idx + 1].token == T_COMMA && tokenarray[idx + 2].token != T_FINAL)
						idx++;
				}
				else {
					return(EmitErr(SYNTAX_ERROR_EX, tokenarray[idx].string_ptr));
				}
			}
		}
		i++;
	}

#if AMD64_SUPPORT

	/* ALL stackbase:rsp and rbp procs will be forced to be FRAME based to ensure consistency and simplicity */
	if (ModuleInfo.basereg[ModuleInfo.Ofssize] == T_RSP || ModuleInfo.basereg[ModuleInfo.Ofssize] == T_RBP)
	{
		/* dont apply this setting to proto,export or when the prologue/epilgoue has been changed by the user or if frame:auto isn't set */
		if (ModuleInfo.prologuemode == PEM_DEFAULT && IsPROC && ModuleInfo.frame_auto == 1)
			proc->e.procinfo->isframe = TRUE;
	}

	/* check for optional FRAME[:exc_proc] */
	if (ModuleInfo.Ofssize == USE64 &&
		IsPROC &&
		tokenarray[i].token == T_RES_ID &&
		tokenarray[i].tokval == T_FRAME) {
		/* v2.05: don't accept FRAME for ELF  - 2016-02-10 John Hankinson allowed ELF64 to use FRAME/Win64 ABI */
		if (Options.output_format != OFORMAT_COFF && Options.output_format != OFORMAT_ELF && Options.output_format != OFORMAT_BIN && Options.output_format != OFORMAT_MAC
#if PE_SUPPORT
			&& ModuleInfo.sub_format != SFORMAT_PE
#endif
			) {
			return(EmitErr(NOT_SUPPORTED_WITH_CURR_FORMAT, GetResWName(T_FRAME, NULL)));
		}
		i++;
		if (tokenarray[i].token == T_COLON) {
			struct asym *sym;
			i++;
			if (tokenarray[i].token != T_ID) {
				return(EmitErr(SYNTAX_ERROR_EX, tokenarray[i].string_ptr));
			}
			sym = SymSearch(tokenarray[i].string_ptr);
			if (sym == NULL) {
				sym = SymCreate(tokenarray[i].string_ptr);
				sym->state = SYM_UNDEFINED;
				sym->used = TRUE;
				sym_add_table(&SymTables[TAB_UNDEF], (struct dsym *)sym); /* add UNDEFINED */
			}
			else if (sym->state != SYM_UNDEFINED &&
				sym->state != SYM_INTERNAL &&
				sym->state != SYM_EXTERNAL) {
				return(EmitErr(SYMBOL_REDEFINITION, sym->name));
			}
			proc->e.procinfo->exc_handler = sym;
			i++;
		}
		else
			proc->e.procinfo->exc_handler = NULL;
		proc->e.procinfo->isframe = TRUE;
	}
#endif
	/* check for USES */
	if (tokenarray[i].token == T_ID && _stricmp(tokenarray[i].string_ptr, "USES") == 0) {
		int cnt;
		int j;
		if (!IsPROC) {/* not for PROTO! */
			DebugMsg(("ParseProc: USES found in PROTO\n"));
			EmitErr(SYNTAX_ERROR_EX, tokenarray[i].string_ptr);
		}
		i++;
		/* count register names which follow */
		for (cnt = 0, j = i; tokenarray[j].token == T_REG; j++, cnt++);

		if (cnt == 0) {
			DebugMsg(("ParseProc: no registers for regslist\n"));
			EmitErr(SYNTAX_ERROR_EX, tokenarray[i - 1].tokpos);
		}
		else {
			regist = LclAlloc((cnt + 1) * sizeof(uint_16));
			proc->e.procinfo->regslist = regist;
			*regist++ = cnt;
			/* read in registers */
			for (; tokenarray[i].token == T_REG; i++) {
				if (SizeFromRegister(tokenarray[i].tokval) == 1) {
					EmitError(INVALID_USE_OF_REGISTER);
				}
				*regist++ = tokenarray[i].tokval;
			}
		}
	}

	/* the parameters must follow */
	if (tokenarray[i].token == T_STYPE || tokenarray[i].token == T_RES_ID || tokenarray[i].token == T_DIRECTIVE) {
		return(EmitErr(SYNTAX_ERROR_EX, tokenarray[i].string_ptr));
	}

	/* skip optional comma */
	if (tokenarray[i].token == T_COMMA)
		i++;

	DebugMsg1(("ParseProc(%s): i=%u, Token_Count=%u, CurrWordSize=%u\n", proc->sym.name, i, Token_Count, CurrWordSize));

	if (i >= Token_Count) {
		/* procedure has no parameters at all */
		if (proc->e.procinfo->paralist != NULL)
			EmitErr(CONFLICTING_PARAMETER_DEFINITION, "");
	}
	else if (proc->sym.langtype == LANG_NONE) {
		EmitError(LANG_MUST_BE_SPECIFIED);
	}
	else {
		/* v2.05: set PROC's vararg flag BEFORE params are scanned! */
		if (tokenarray[Token_Count - 1].token == T_RES_ID &&
			tokenarray[Token_Count - 1].tokval == T_VARARG)
			proc->e.procinfo->has_vararg = TRUE;
		/* v2.04: removed, comma is checked above already */
		//if( tokenarray[i].token == T_COMMA )
		//    i++;
		if (ERROR == ParseParams(proc, i, tokenarray, IsPROC))
			/* do proceed if the parameter scan returns an error */
			;//return( ERROR );
	}

	/* v2.11: isdefined and isproc now set here */
	proc->sym.isdefined = TRUE;
	proc->sym.isproc = TRUE;
	//proc->e.procinfo->init_done = TRUE;
	DebugMsg1(("ParseProc(%s): memtype=%Xh parasize=%u\n", proc->sym.name, proc->sym.mem_type, proc->e.procinfo->parasize));

	return(NOT_ERROR);
}

/* create a proc ( internal[=PROC] or external[=PROTO] ) item.
* sym is either NULL, or has type SYM_UNDEFINED or SYM_EXTERNAL.
* called by:
* - ProcDir ( state == SYM_INTERNAL )
* - CreateLabel ( state == SYM_INTERNAL )
* - AddLinnumDataRef ( state == SYM_INTERNAL, sym==NULL )
* - CreateProto ( state == SYM_EXTERNAL )
* - ExterndefDirective ( state == SYM_EXTERNAL )
* - ExternDirective ( state == SYM_EXTERNAL )
* - TypedefDirective ( state == SYM_TYPE, sym==NULL )
*/
struct asym *CreateProc(struct asym *sym, const char *name, enum sym_state state)
	/*********************************************************************************/
{
	if (sym == NULL)
		sym = (*name ? SymCreate(name) : SymAlloc(name));
	else
		sym_remove_table((sym->state == SYM_UNDEFINED) ? &SymTables[TAB_UNDEF] : &SymTables[TAB_EXT], (struct dsym *)sym);

	if (sym) {
		struct proc_info *info;
		sym->state = state;
		if (state != SYM_INTERNAL) {
			sym->seg_ofssize = ModuleInfo.Ofssize;
		}
		info = LclAlloc(sizeof(struct proc_info));
		((struct dsym *)sym)->e.procinfo = info;
		info->regslist = NULL;
		info->paralist = NULL;
		info->locallist = NULL;
		info->labellist = NULL;
		info->parasize = 0;
		info->localsize = 0;
		info->prologuearg = NULL;
		info->flags = 0;
		info->ret_type = 0xff;
		switch (sym->state) {
		case SYM_INTERNAL:
			/* v2.04: don't use sym_add_table() and thus
			* free the <next> member field!
			*/
			if (SymTables[TAB_PROC].head == NULL)
				SymTables[TAB_PROC].head = (struct dsym *)sym;
			else {
				SymTables[TAB_PROC].tail->nextproc = (struct dsym *)sym;
			}
			SymTables[TAB_PROC].tail = (struct dsym *)sym;
			procidx++;
			if (Options.line_numbers) {
				sym->debuginfo = LclAlloc(sizeof(struct debug_info));
				sym->debuginfo->file = get_curr_srcfile();
			}
			break;
		case SYM_EXTERNAL:
			sym->weak = TRUE;
			sym_add_table(&SymTables[TAB_EXT], (struct dsym *)sym);
			break;
		}
	}
	return(sym);
}

/* delete a PROC item */
void DeleteProc(struct dsym *proc)
/**********************************/
{
	struct dsym *curr;
	struct dsym *next;

	DebugMsg(("DeleteProc(%s) enter\n", proc->sym.name));
	if (proc->sym.state == SYM_INTERNAL) {

		/* delete all local symbols ( params, locals, labels ) */
		for (curr = proc->e.procinfo->labellist; curr; ) {
			next = curr->e.nextll;
			DebugMsg(("DeleteProc(%s): free %s [next=%p]\n", proc->sym.name, curr->sym.name, curr->next));
			SymFree(&curr->sym);
			curr = next;
		}

		if (proc->e.procinfo->regslist)
			LclFree(proc->e.procinfo->regslist);

		if (proc->e.procinfo->prologuearg)
			LclFree(proc->e.procinfo->prologuearg);

		if (Options.line_numbers && proc->sym.state == SYM_INTERNAL)
			LclFree(proc->sym.debuginfo);
#if FASTMEM==0 || defined(DEBUG_OUT)
	}
	else {
		/* PROTOs have just a parameter list, usually without names */
		for (curr = proc->e.procinfo->paralist; curr; ) {
			next = curr->nextparam;
			DebugMsg(("DeleteProc(%s): free %p (%s) [next=%p]\n", proc->sym.name, curr, curr->sym.name, curr->next));
			SymFree(&curr->sym);
			curr = next;
		}
#endif
	}
	LclFree(proc->e.procinfo);
	return;
}

/* PROC directive. */
ret_code ProcDir(int i, struct asm_tok tokenarray[])
/****************************************************/
{
	struct asym         *sym;
	unsigned int        ofs;
	char                *name;
	bool                oldpubstate;
	bool                is_global;
	struct asym*        cline;
	struct asym*        procline;
	struct asym*        procname;

	/* Store the current source code line relating to the PROC */
	cline = SymFind("@Line");
	procline = SymFind("@ProcLine");
	procline->value = cline->value;

	DebugMsg1(("ProcDir enter, curr ofs=%X\n", GetCurrOffset()));
	if (i != 1) {
		return(EmitErr(SYNTAX_ERROR_EX, tokenarray[i].string_ptr));
	}
	/* v2.04b: check was missing */
	if (CurrSeg == NULL) {
		return(EmitError(MUST_BE_IN_SEGMENT_BLOCK));
	}

	name = tokenarray[0].string_ptr;

	if (CurrProc != NULL) {

		/* Set the current PROC name */
		procname = SymFind("@ProcName");
		procname->string_ptr = CurrProc->sym.name;

		/* this is not needed for Uasm, but Masm will reject nested
		* procs if there are params, locals or used registers.
		*/
		if (CurrProc->e.procinfo->paralist ||
#if AMD64_SUPPORT
			CurrProc->e.procinfo->isframe ||
#endif
			CurrProc->e.procinfo->locallist ||
			CurrProc->e.procinfo->regslist) {
			return(EmitErr(CANNOT_NEST_PROCEDURES, name));
		}
		/* nested procs ... push currproc on a stack */
		push_proc(CurrProc);
	}


	if (ModuleInfo.procalign) {
		AlignCurrOffset(ModuleInfo.procalign);
	}

	i++; /* go past PROC */

	sym = SymSearch(name);

	if (Parse_Pass == PASS_1) { //|| (Parse_Pass > PASS_1 && sym == NULL) ) {

		oldpubstate = sym ? sym->ispublic : FALSE;
		if (sym == NULL || sym->state == SYM_UNDEFINED) {
			sym = CreateProc(sym, name, SYM_INTERNAL);
			is_global = FALSE;
		}
		else if (sym->state == SYM_EXTERNAL && sym->weak == TRUE) {
			/* PROTO or EXTERNDEF item */
			is_global = TRUE;
			if (sym->isproc == TRUE) {
				/* don't create the procinfo extension; it exists already */
				procidx++; /* v2.04: added */
				if (Options.line_numbers) {
					sym->debuginfo = LclAlloc(sizeof(struct debug_info));
					sym->debuginfo->file = get_curr_srcfile();
				}
			}
			else {
				/* it's a simple EXTERNDEF. Create a PROC item!
				* this will be SYM_INTERNAL */
				/* v2.03: don't call dir_free(), it'll clear field Ofssize */
				//dir_free( (struct dsym *)sym );
				sym = CreateProc(sym, name, SYM_INTERNAL);
			}
		}
		else {
			/* Masm won't reject a redefinition if "certain" parameters
			* won't change. However, in a lot of cases one gets "internal assembler error".
			* Hence this "feature" isn't active in Uasm.
			*/
			//} else if ( sym->state != SYM_INTERNAL || sym->isproc != TRUE ||
			//           sym->offset != GetCurrOffset() || sym->segment != &CurrSeg->sym ) {
			return(EmitErr(SYMBOL_REDEFINITION, sym->name));
		}
		SetSymSegOfs(sym);

		SymClearLocal();

#if STACKBASESUPP
		/* v2.11: added. Note that fpo flag is only set if there ARE params! */
		((struct dsym *)sym)->e.procinfo->basereg = ModuleInfo.basereg[ModuleInfo.Ofssize];
#endif
		/* CurrProc must be set, it's used inside SymFind() and SymLCreate()! */
		CurrProc = (struct dsym *)sym;
		if (ParseProc((struct dsym *)sym, i, tokenarray, TRUE, ModuleInfo.langtype) == ERROR) {
			CurrProc = NULL;
			return(ERROR);
		}
		/* v2.04: added */
		if (is_global && Options.masm8_proc_visibility)
			sym->ispublic = TRUE;

		/* if there was a PROTO (or EXTERNDEF name:PROTO ...),
		* change symbol to SYM_INTERNAL!
		*/
		if (sym->state == SYM_EXTERNAL && sym->isproc == TRUE) {
			sym_ext2int(sym);
			/* v2.11: added ( may be better to call CreateProc() - currently not possible ) */
			if (SymTables[TAB_PROC].head == NULL)
				SymTables[TAB_PROC].head = (struct dsym *)sym;
			else {
				SymTables[TAB_PROC].tail->nextproc = (struct dsym *)sym;
			}
			SymTables[TAB_PROC].tail = (struct dsym *)sym;
		}

		/* v2.11: sym->isproc is set inside ParseProc() */
		//sym->isproc = TRUE;
#if STACKBASESUPP
		/* v2.11: Note that fpo flag is only set if there ARE params ( or locals )! */
		if (CurrProc->e.procinfo->paralist && GetRegNo(CurrProc->e.procinfo->basereg) == 4)
			CurrProc->e.procinfo->fpo = TRUE;
#endif
		if (sym->ispublic == TRUE && oldpubstate == FALSE)
			AddPublicData(sym);

		/* v2.04: add the proc to the list of labels attached to curr segment.
		* this allows to reduce the number of passes (see fixup.c)
		*/
		((struct dsym *)sym)->next = (struct dsym *)CurrSeg->e.seginfo->label_list;
		CurrSeg->e.seginfo->label_list = sym;

	}
	else {

		procidx++;
		sym->isdefined = TRUE;

		SymSetLocal(sym);

		/* it's necessary to check for a phase error here
		as it is done in LabelCreate() and data_dir()!
		*/
		ofs = GetCurrOffset();

		if (ofs != sym->offset) {
			sym->offset = ofs;
			ModuleInfo.PhaseError = TRUE;
		}
		CurrProc = (struct dsym *)sym;

		/* check if the exception handler set by FRAME is defined */
		if (CurrProc->e.procinfo->isframe &&
			CurrProc->e.procinfo->exc_handler &&
			CurrProc->e.procinfo->exc_handler->state == SYM_UNDEFINED) {
			EmitErr(SYMBOL_NOT_DEFINED, CurrProc->e.procinfo->exc_handler->name);
		}
	}

	/* v2.11: init @ProcStatus - prologue not written yet, optionally set FPO flag */
#if STACKBASESUPP
	ProcStatus = PRST_PROLOGUE_NOT_DONE | (CurrProc->e.procinfo->fpo ? PRST_FPO : 0);
	StackAdj = 0;  /* init @StackBase to 0 */
	StackAdjHigh = 0;
#else
	ProcStatus = PRST_PROLOGUE_NOT_DONE;
#endif

#if AMD64_SUPPORT
	if (CurrProc->e.procinfo->isframe) {
		endprolog_found = FALSE;
		/* v2.11: clear all fields */
		memset(&unw_info, 0, sizeof(unw_info));
		if (CurrProc->e.procinfo->exc_handler)
			unw_info.Flags = UNW_FLAG_FHANDLER;
	}
#endif

	sym->asmpass = Parse_Pass;
	if (ModuleInfo.list)
		LstWrite(LSTTYPE_LABEL, 0, NULL);

	if (Options.line_numbers) {
		if (Options.debug_symbols == 4)
			AddLinnumDataRef(get_curr_srcfile(), GetLineNumber());
		else
			AddLinnumDataRef(get_curr_srcfile(), Options.output_format == OFORMAT_COFF ? 0 : GetLineNumber());
	}

	BackPatch(sym);
	return(NOT_ERROR);
}

ret_code CopyPrototype(struct dsym *proc, struct dsym *src)
/***********************************************************/
{
	struct dsym *curr;
	struct dsym *newl;
	struct dsym *oldl;

	if (src->sym.isproc == FALSE)
		return(ERROR);
	memcpy(proc->e.procinfo, src->e.procinfo, sizeof(struct proc_info));
	proc->sym.mem_type = src->sym.mem_type;
	proc->sym.langtype = src->sym.langtype;
#if MANGLERSUPP
	proc->sym.mangler = src->sym.mangler;
#endif
	proc->sym.ispublic = src->sym.ispublic;
	/* we use the PROTO part, not the TYPE part */
	//dir->sym.seg_ofssize = src->sym.Ofssize;
	proc->sym.seg_ofssize = src->sym.seg_ofssize;
	proc->sym.isproc = TRUE;
	proc->e.procinfo->paralist = NULL;
	for (curr = src->e.procinfo->paralist; curr; curr = curr->nextparam) {
		newl = LclAlloc(sizeof(struct dsym));
		memcpy(newl, curr, sizeof(struct dsym));
		newl->nextparam = NULL;
		if (proc->e.procinfo->paralist == NULL)
			proc->e.procinfo->paralist = newl;
		else {
			for (oldl = proc->e.procinfo->paralist; oldl->nextparam; oldl = oldl->nextparam);
			oldl->nextparam = newl;
		}
	}
	DebugMsg1(("CopyPrototype(%s,src=%s): ofssize=%u\n",
		proc->sym.name, src->sym.name, src->sym.seg_ofssize));
	return(NOT_ERROR);
}

/* close a PROC */
static void ProcFini(struct dsym *proc)
/***************************************/
{
	struct asym* procline = NULL;
	struct dsym *curr;
	/* v2.06: emit an error if current segment isn't equal to
	* the one of the matching PROC directive. Close the proc anyway!
	*/
	if (proc->sym.segment == &CurrSeg->sym) {
		proc->sym.total_size = GetCurrOffset() - proc->sym.offset;
	}
	else {
		DebugMsg1(("ProcFini(%s): unmatched block nesting error, proc->seg=%s, CurrSeg=%s\n",
			proc->sym.name, proc->sym.segment->name, CurrSeg ? CurrSeg->sym.name : "NULL"));
		EmitErr(UNMATCHED_BLOCK_NESTING, proc->sym.name);
		proc->sym.total_size = CurrProc->sym.segment->offset - proc->sym.offset;
	}

	/* v2.03: for W3+, check for unused params and locals */
	if (Options.warning_level > 2 && Parse_Pass == PASS_1) {
		for (curr = proc->e.procinfo->paralist; curr; curr = curr->nextparam) {
			if (curr->sym.used == FALSE)
				EmitWarn(3, PROCEDURE_ARGUMENT_OR_LOCAL_NOT_REFERENCED, curr->sym.name);
		}
		for (curr = proc->e.procinfo->locallist; curr; curr = curr->nextlocal) {
			if (curr->sym.used == FALSE)
				EmitWarn(3, PROCEDURE_ARGUMENT_OR_LOCAL_NOT_REFERENCED, curr->sym.name);
		}
	}
#if AMD64_SUPPORT
	/* save stack space reserved for INVOKE if OPTION WIN64:2 is set */
	if (Parse_Pass == PASS_1 &&
		ModuleInfo.fctype == FCT_WIN64 &&
		(ModuleInfo.win64_flags & W64F_AUTOSTACKSP)) {
		proc->e.procinfo->ReservedStack = sym_ReservedStack->value;
		DebugMsg1(("ProcFini(%s): localsize=%u ReservedStack=%u\n", proc->sym.name, proc->e.procinfo->localsize, proc->e.procinfo->ReservedStack));
#if STACKBASESUPP
		if (proc->e.procinfo->fpo) {
			if (proc->e.procinfo->ReservedStack > 0)
			{
				for (curr = proc->e.procinfo->locallist; curr; curr = curr->nextlocal) {
					DebugMsg1(("ProcFini(%s): FPO, offset for %s %8d -> %8d\n", proc->sym.name, curr->sym.name, curr->sym.offset, curr->sym.offset + proc->e.procinfo->ReservedStack));
					curr->sym.offset += proc->e.procinfo->ReservedStack;
				}
				for (curr = proc->e.procinfo->paralist; curr; curr = curr->nextparam) {
					DebugMsg1(("ProcFini(%s): FPO, offset for %s %8d -> %8d\n", proc->sym.name, curr->sym.name, curr->sym.offset, curr->sym.offset + proc->e.procinfo->ReservedStack));
					curr->sym.offset += proc->e.procinfo->ReservedStack;
				}
			}
		}
#endif
	}

	/* create the .pdata and .xdata stuff */
	if (proc->e.procinfo->isframe)
	{
#if FASTPASS
		LstSetPosition(); /* needed if generated code is done BEFORE the line is listed */
#endif
		if(proc->sym.langtype != LANG_SYSVCALL)
			WriteSEHData(proc);
	}
#endif
	if (ModuleInfo.list)
		LstWrite(LSTTYPE_LABEL, 0, NULL);

	/* create the list of locals */
	if (Parse_Pass == PASS_1) {
		/* in case the procedure is empty, init addresses of local variables ( for proper listing ) */
		if (ProcStatus & PRST_PROLOGUE_NOT_DONE) {
			if (ModuleInfo.basereg[USE64] == T_RSP) {
				SetLocalOffsets_RSP(CurrProc->e.procinfo);
			}
			else if (proc->sym.langtype == LANG_SYSVCALL) {
				SetLocalOffsets_RBP_SYSV(CurrProc->e.procinfo);
			}
			else {
				SetLocalOffsets_RBP(CurrProc->e.procinfo);
			}
		}
		SymGetLocal((struct asym *)CurrProc);
	}

	/* UASM 2.49 Ensure ProcLine value is reset */
	procline = SymFind("@ProcLine");
	procline->value = 0;

	CurrProc = pop_proc();
	if (CurrProc)
		SymSetLocal((struct asym *)CurrProc);  /* restore local symbol table */

	ProcStatus = 0; /* in case there was an empty PROC/ENDP pair */
	if (sym_ReservedStack)
		sym_ReservedStack->value = 0;
}

/* ENDP directive */
ret_code EndpDir(int i, struct asm_tok tokenarray[])
/****************************************************/
{
	struct asym*        procline;

	DebugMsg1(("EndpDir(%s) enter, curr ofs=% " I32_SPEC "X, CurrProc=%s\n", tokenarray[0].string_ptr, GetCurrOffset(), CurrProc ? CurrProc->sym.name : "NULL"));
	if (i != 1 || tokenarray[2].token != T_FINAL) {
		return(EmitErr(SYNTAX_ERROR_EX, tokenarray[i].tokpos));
	}
	/* v2.10: "+ 1" added to CurrProc->sym.name_size */
	if (CurrProc &&
		(SymCmpFunc(CurrProc->sym.name, tokenarray[0].string_ptr, CurrProc->sym.name_size + 1) == 0)) {

		/* Reset the current source code line relating to the PROC */
		procline = SymFind("@ProcLine");
		procline->value = 0;

		ProcFini(CurrProc);
	}
	else {
		return(EmitErr(UNMATCHED_BLOCK_NESTING, tokenarray[0].string_ptr));
	}
	return(NOT_ERROR);
}

#if AMD64_SUPPORT

/* for FRAME procs, write .pdata and .xdata SEH unwind information */
static void WriteSEHData(struct dsym *proc)
/*******************************************/
{
	struct dsym *xdata;
	char *segname = ".xdata";
	int i;
	int simplespec;
	uint_8 olddotname;
	uint_32 xdataofs = 0;
	char segnamebuff[12];
	char buffer[128];

	/* 2016-02-10 John Hankinson - Don't bother writing SEH data for ELF64, MACHO64 or Uasm flat mode even if it was generated */
	if (Options.output_format == OFORMAT_ELF || Options.output_format == OFORMAT_BIN || Options.output_format == OFORMAT_MAC)
		return;

	if (endprolog_found == FALSE) {
		EmitErr(MISSING_ENDPROLOG, proc->sym.name);
	}
	if (unw_segs_defined)
		AddLineQueueX("%s %r", segname, T_SEGMENT);
	else {
		AddLineQueueX("%s %r align(%u) flat read 'DATA'", segname, T_SEGMENT, 8);
		AddLineQueue("$xdatasym label near");
	}
	xdataofs = 0;
	xdata = (struct dsym *)SymSearch(segname);
	if (xdata) {
		/* v2.11: changed offset to max_offset.
		* However, value structinfo.current_loc might even be better.
		*/
		xdataofs = xdata->sym.max_offset;
	}

	/* write the .xdata stuff (a UNWIND_INFO entry )
	* v2.11: 't'-suffix added to ensure the values are correct if radix is != 10.
	*/
	AddLineQueueX("db %ut + (0%xh shl 3), %ut, %ut, 0%xh + (0%xh shl 4)",
		UNW_VERSION, unw_info.Flags, unw_info.SizeOfProlog,
		unw_info.CountOfCodes, unw_info.FrameRegister, unw_info.FrameOffset);
	if (unw_info.CountOfCodes) {
		char *pfx = "dw";
		buffer[0] = NULLC;
		/* write the codes from right to left */
		for (i = unw_info.CountOfCodes; i; i--) {
			/* v2.11: use field FrameOffset */
			//sprintf( buffer + strlen( buffer ), "%s 0%xh", pfx, unw_code[i-1] );
			sprintf(buffer + strlen(buffer), "%s 0%xh", pfx, unw_code[i - 1].FrameOffset);
			pfx = ",";
			if (i == 1 || strlen(buffer) > 72) {
				AddLineQueue(buffer);
				buffer[0] = NULLC;
				pfx = "dw";
			}
		}
	}
	/* make sure the unwind codes array has an even number of entries */
	AddLineQueueX("%r 4", T_ALIGN);

	if (proc->e.procinfo->exc_handler) {
		AddLineQueueX("dd %r %s", T_IMAGEREL, proc->e.procinfo->exc_handler->name);
		//AddLineQueueX("%r 8", T_ALIGN);
		AddLineQueueX("dd 0"); // This matches ML64 output (but is probably less space efficient) -> UASM 2.44
	}
	AddLineQueueX("%s %r", segname, T_ENDS);

	/* v2.07: ensure that .pdata items are sorted */
	if (0 == strcmp(SimGetSegName(SIM_CODE), proc->sym.segment->name)) {
		segname = ".pdata";
		simplespec = (unw_segs_defined & 1);
		unw_segs_defined = 3;
	}
	else {
		segname = segnamebuff;
		sprintf(segname, ".pdata$%04u", GetSegIdx(proc->sym.segment));
		simplespec = 0;
		unw_segs_defined |= 2;
	}

	if (simplespec)
		AddLineQueueX("%s %r", segname, T_SEGMENT);
	else
		AddLineQueueX("%s %r align(%u) flat read 'DATA'", segname, T_SEGMENT, 4);
	/* write the .pdata stuff ( type IMAGE_RUNTIME_FUNCTION_ENTRY )*/
	AddLineQueueX("dd %r %s, %r %s+0%xh, %r $xdatasym+0%xh",
		T_IMAGEREL, proc->sym.name,
		T_IMAGEREL, proc->sym.name, proc->sym.total_size,
		T_IMAGEREL, xdataofs);
	AddLineQueueX("%s %r", segname, T_ENDS);
	olddotname = ModuleInfo.dotname;
	ModuleInfo.dotname = TRUE; /* set OPTION DOTNAME because .pdata and .xdata */
	RunLineQueue();
	ModuleInfo.dotname = olddotname;
	return;
}

/* handles win64 directives
* .allocstack
* .endprolog
* .pushframe
* .pushreg
* .savereg
* .savexmm128
* .setframe
*/
ret_code ExcFrameDirective(int i, struct asm_tok tokenarray[])
/**************************************************************/
{
	struct expr opndx;
	int token;
	unsigned int size;
	uint_8 oldcodes = unw_info.CountOfCodes;
	uint_8 reg;
	uint_8 ofs;
	UNWIND_CODE *puc;

	DebugMsg1(("ExcFrameDirective(%s) enter\n", tokenarray[i].string_ptr));
	/* v2.05: accept directives for windows only (UASM 2.45 allows these with other formats like elf/mac/bin even though they'll be ignored) */
	if (Options.output_format != OFORMAT_COFF && Options.output_format != OFORMAT_ELF && Options.output_format != OFORMAT_BIN && Options.output_format != OFORMAT_MAC
#if PE_SUPPORT
		&& ModuleInfo.sub_format != SFORMAT_PE
#endif
		) {
		return(EmitErr(NOT_SUPPORTED_WITH_CURR_FORMAT, GetResWName(tokenarray[i].tokval, NULL)));
	}
	if (CurrProc == NULL || endprolog_found == TRUE) {
		return(EmitError(ENDPROLOG_FOUND_BEFORE_EH_DIRECTIVES));
	}
	if (CurrProc->e.procinfo->isframe == FALSE) {
		return(EmitError(MISSING_FRAME_IN_PROC));
	}

	puc = &unw_code[unw_info.CountOfCodes];

	ofs = GetCurrOffset() - CurrProc->sym.offset;
	token = tokenarray[i].tokval;
	i++;

	/* note: since the codes will be written from "right to left",
	* the opcode item has to be written last!
	*/

	switch (token) {
	case T_DOT_ALLOCSTACK: /* syntax: .ALLOCSTACK size */
		if (ERROR == EvalOperand(&i, tokenarray, Token_Count, &opndx, 0))
			return(ERROR);
		if (opndx.kind == EXPR_ADDR && opndx.sym->state == SYM_UNDEFINED) /* v2.11: allow forward references */
			;
		else if (opndx.kind != EXPR_CONST) {
			return(EmitError(CONSTANT_EXPECTED));
		}
		/* v2.11: check added */
		if (opndx.hvalue) {
			return(EmitConstError(&opndx));
		}
		if (opndx.uvalue == 0) {
			return(EmitError(NONZERO_VALUE_EXPECTED));
		}
		if (opndx.value & 7) {
			return(EmitError(BAD_ALIGNMENT_FOR_OFFSET_IN_UNWIND_CODE));
		}
		//opndx.value -= 8; /* v2.11: subtract 8 only for UWOP_ALLOC_SMALL! */
		if (opndx.uvalue > 16 * 8) {
			if (opndx.uvalue >= 65536 * 8) {
				/* allocation size 512k - 4G-8 */
				/* v2.11: value is stored UNSCALED in 2 WORDs! */
				puc->FrameOffset = (opndx.uvalue >> 16);
				puc++;
				puc->FrameOffset = opndx.uvalue & 0xFFFF;
				puc++;
				unw_info.CountOfCodes += 2;
				puc->OpInfo = 1;
				DebugMsg1(("ExcFrameDirective: UWOP_ALLOC_LARGE, operation info 1, size=%Xh\n", opndx.value));
			}
			else {
				/* allocation size 128+8 - 512k-8 */
				puc->FrameOffset = (opndx.uvalue >> 3);
				puc++;
				unw_info.CountOfCodes++;
				puc->OpInfo = 0;
				DebugMsg1(("ExcFrameDirective: UWOP_ALLOC_LARGE, operation info 0, size=%Xh\n", opndx.value));
			}
			puc->UnwindOp = UWOP_ALLOC_LARGE;
		}
		else {
			/* allocation size 8-128 bytes */
			puc->UnwindOp = UWOP_ALLOC_SMALL;
			/* v2.11: subtract 8 only for UWOP_ALLOC_SMALL! */
			//puc->OpInfo = ( opndx.value >> 3 );
			puc->OpInfo = ((opndx.uvalue - 8) >> 3);
			DebugMsg1(("ExcFrameDirective: UWOP_ALLOC_SMALL, size=%Xh\n", opndx.value));
		}
		puc->CodeOffset = ofs;
		unw_info.CountOfCodes++;
		break;
	case T_DOT_ENDPROLOG: /* syntax: .ENDPROLOG */
		opndx.value = GetCurrOffset() - CurrProc->sym.offset;
		if (opndx.uvalue > 255) {
			return(EmitError(SIZE_OF_PROLOG_TOO_BIG));
		}
		unw_info.SizeOfProlog = (uint_8)opndx.uvalue;
		endprolog_found = TRUE;
		break;
	case T_DOT_PUSHFRAME: /* syntax: .PUSHFRAME [code] */
		puc->CodeOffset = ofs;
		puc->UnwindOp = UWOP_PUSH_MACHFRAME;
		puc->OpInfo = 0;
		if (tokenarray[i].token == T_ID && (_stricmp(tokenarray[i].string_ptr, "CODE") == 0)) {
			puc->OpInfo = 1;
			i++;
		}
		unw_info.CountOfCodes++;
		break;
	case T_DOT_PUSHREG: /* syntax: .PUSHREG r64 */
		if (tokenarray[i].token != T_REG || !(GetValueSp(tokenarray[i].tokval) & OP_R64)) {
			return(EmitErr(SYNTAX_ERROR_EX, tokenarray[i].string_ptr));
		}
		puc->CodeOffset = ofs;
		puc->UnwindOp = UWOP_PUSH_NONVOL;
		puc->OpInfo = GetRegNo(tokenarray[i].tokval);
		unw_info.CountOfCodes++;
		i++;
		break;
	case T_DOT_SAVEREG:    /* syntax: .SAVEREG r64, offset       */
	case T_DOT_SAVEXMM128: /* syntax: .SAVEXMM128 xmmreg, offset */
	case T_DOT_SAVEYMM256: /* syntax: .SAVEYMM256 ymmreg, offset */
	case T_DOT_SAVEZMM512: /* syntax: .SAVEXMM512 zmmreg, offset */
	case T_DOT_SETFRAME:   /* syntax: .SETFRAME r64, offset      */
		if (tokenarray[i].token != T_REG) {
			return(EmitErr(SYNTAX_ERROR_EX, tokenarray[i].string_ptr));
		}
		if (token == T_DOT_SAVEXMM128) {
			if (!(GetValueSp(tokenarray[i].tokval) & OP_XMM)) {
				return(EmitErr(SYNTAX_ERROR_EX, tokenarray[i].string_ptr));
			}
		}
		else if (token == T_DOT_SAVEYMM256) {
			if (!(GetValueSp(tokenarray[i].tokval) & OP_YMM)) {
				return(EmitErr(SYNTAX_ERROR_EX, tokenarray[i].string_ptr));
			}
		}
		else if (token == T_DOT_SAVEZMM512) {
			if (!(GetValueSp(tokenarray[i].tokval) & OP_ZMM)) {
				return(EmitErr(SYNTAX_ERROR_EX, tokenarray[i].string_ptr));
			}
		}
		else {
			if (!(GetValueSp(tokenarray[i].tokval) & OP_R64)) {
				return(EmitErr(SYNTAX_ERROR_EX, tokenarray[i].string_ptr));
			}
		}
		reg = GetRegNo(tokenarray[i].tokval);
		if (token == T_DOT_SAVEREG)
			size = 8;
		else
			size = 16;

		i++;
		if (tokenarray[i].token != T_COMMA) {
			return(EmitErr(SYNTAX_ERROR_EX, tokenarray[i].string_ptr));
		}
		i++;
		if (ERROR == EvalOperand(&i, tokenarray, Token_Count, &opndx, 0))
			return(ERROR);
		if (opndx.kind == EXPR_ADDR && opndx.sym->state == SYM_UNDEFINED) /* v2.11: allow forward references */
			;
		else if (opndx.kind != EXPR_CONST) {
			return(EmitError(CONSTANT_EXPECTED));
		}
		if (opndx.value & (size - 1)) {
			return(EmitError(BAD_ALIGNMENT_FOR_OFFSET_IN_UNWIND_CODE));
		}
		switch (token) {
		case T_DOT_SAVEREG:
			puc->OpInfo = reg;
			if (opndx.value > 65536 * size) {
				puc->FrameOffset = (opndx.value >> 19);
				puc++;
				puc->FrameOffset = (opndx.value >> 3);
				puc++;
				puc->UnwindOp = UWOP_SAVE_NONVOL_FAR;
				unw_info.CountOfCodes += 3;
			}
			else {
				puc->FrameOffset = (opndx.value >> 3);
				puc++;
				puc->UnwindOp = UWOP_SAVE_NONVOL;
				unw_info.CountOfCodes += 2;
			}
			puc->CodeOffset = ofs;
			puc->OpInfo = reg;
			break;
		case T_DOT_SAVEXMM128:
		case T_DOT_SAVEYMM256:
			if (opndx.value > 65536 * size) {
				puc->FrameOffset = (opndx.value >> 20);
				puc++;
				puc->FrameOffset = (opndx.value >> 4);
				puc++;
				puc->UnwindOp = UWOP_SAVE_XMM128_FAR;
				unw_info.CountOfCodes += 3;
			}
			else {
				puc->FrameOffset = (opndx.value >> 4);
				puc++;
				puc->UnwindOp = UWOP_SAVE_XMM128;
				unw_info.CountOfCodes += 2;
			}
			puc->CodeOffset = ofs;
			puc->OpInfo = reg;
			break;
			//case T_DOT_SAVEYMM256:
			//    if ( opndx.value > 65536 * size ) {
			//        puc->FrameOffset = ( opndx.value >> 20 );
			//        puc++;
			//        puc->FrameOffset = ( opndx.value >> 4 );
			//        puc++;
			//        puc->UnwindOp = UWOP_SAVE_YMM256_FAR;
			//        unw_info.CountOfCodes += 3;
			//    } else {
			//        puc->FrameOffset = ( opndx.value >> 4 );
			//        puc++;
			//        puc->UnwindOp = UWOP_SAVE_YMM256;
			//        unw_info.CountOfCodes += 2;
			//    }
			//    puc->CodeOffset = ofs;
			//    puc->OpInfo = reg;
			//    break;
		case T_DOT_SAVEZMM512:
			if (opndx.value > 65536 * size) {
				puc->FrameOffset = (opndx.value >> 20);
				puc++;
				puc->FrameOffset = (opndx.value >> 4);
				puc++;
				puc->UnwindOp = UWOP_SAVE_XMM128_FAR;
				unw_info.CountOfCodes += 3;
			}
			else {
				puc->FrameOffset = (opndx.value >> 4);
				puc++;
				puc->UnwindOp = UWOP_SAVE_XMM128;
				unw_info.CountOfCodes += 2;
			}
			puc->CodeOffset = ofs;
			puc->OpInfo = reg;
			break;
		case T_DOT_SETFRAME:
			if (opndx.uvalue > 240) {
				return(EmitConstError(&opndx));
			}
			unw_info.FrameRegister = reg;
			unw_info.FrameOffset = (opndx.uvalue >> 4);
			puc->CodeOffset = ofs;
			puc->UnwindOp = UWOP_SET_FPREG;
			//puc->OpInfo = ( opndx.uvalue >> 4 );
			puc->OpInfo = reg;
			unw_info.CountOfCodes++;
			break;
		}
		break;
	}
	if (tokenarray[i].token != T_FINAL) {
		return(EmitErr(SYNTAX_ERROR_EX, tokenarray[i].string_ptr));
	}
	/* v2.11: check if the table of codes has been exceeded */
	if (oldcodes > unw_info.CountOfCodes) {
		return(EmitErr(TOO_MANY_UNWIND_CODES_IN_FRAME_PROC));
	}
	return(NOT_ERROR);
}

#endif

/* see if there are open procedures.
* called when the END directive has been found.
*/
void ProcCheckOpen(void)
/************************/
{
	while (CurrProc != NULL) {
		DebugMsg1(("ProcCheckOpen: unmatched block nesting error, CurrProc=%s\n", CurrProc->sym.name));
		EmitErr(UNMATCHED_BLOCK_NESTING, CurrProc->sym.name);
		ProcFini(CurrProc);
	}
}

static ret_code write_userdef_prologue(struct asm_tok tokenarray[])
/*******************************************************************/
{
	int                 len;
	int                 i;
	struct proc_info    *info;
	char                *p;
	bool                is_exitm;
	struct dsym         *dir;
	//int                 align = CurrWordSize;
	int                 flags = CurrProc->sym.langtype; /* set bits 0-2 */
	uint_16             *regs;
	char                reglst[128];
	char                buffer[MAX_LINE_LEN];
	//struct asym         *cline;
	//int                 curline;

#if FASTPASS
	if (Parse_Pass > PASS_1 && UseSavedState)
		return(NOT_ERROR);
#endif

	info = CurrProc->e.procinfo;
	/* v2.11: now done in write_prologue() */
	//info->localsize = ROUND_UP( info->localsize, CurrWordSize );
#if AMD64_SUPPORT
	/* to be compatible with ML64, translate FASTCALL to 0 (not 7) */
	if (CurrProc->sym.langtype == LANG_FASTCALL && ModuleInfo.fctype == FCT_WIN64)
		flags = 0;
#endif
	/* set bit 4 if the caller restores (E)SP */
	if (CurrProc->sym.langtype == LANG_C ||
		CurrProc->sym.langtype == LANG_SYSCALL ||
		CurrProc->sym.langtype == LANG_SYSVCALL ||
		CurrProc->sym.langtype == LANG_FASTCALL)
		flags |= 0x10;

	/* set bit 5 if proc is far */
	/* set bit 6 if proc is private */
	/* v2.11: set bit 7 if proc is export */
	flags |= (CurrProc->sym.mem_type == MT_FAR ? 0x20 : 0);
	flags |= (CurrProc->sym.ispublic ? 0 : 0x40);
	flags |= (info->isexport ? 0x80 : 0);

	dir = (struct dsym *)SymSearch(ModuleInfo.proc_prologue);
	if (dir == NULL || dir->sym.state != SYM_MACRO || dir->sym.isfunc != TRUE) {
		return(EmitError(PROLOGUE_MUST_BE_MACRO_FUNC));
	}

	/* if -EP is on, emit "prologue: none" */
	if (Options.preprocessor_stdout)
		printf("option prologue:none\n");

	p = reglst;
	if (info->regslist) {
		regs = info->regslist;
		for (len = *regs++; len; len--, regs++) {
			GetResWName(*regs, p);
			p += strlen(p);
			if (len > 1)
				*p++ = ',';
		}
	}
	*p = NULLC;

	/* v2.07: make this work with radix != 10 */
	/* leave a space at pos 0 of buffer, because the buffer is used for
	* both macro arguments and EXITM return value.
	*/
	sprintf(buffer, " (%s, 0%XH, 0%XH, 0%XH, <<%s>>, <%s>)",
		CurrProc->sym.name, flags, info->parasize, info->localsize,
		reglst, info->prologuearg ? info->prologuearg : "");
	i = Token_Count + 1;
	Token_Count = Tokenize(buffer, i, tokenarray, TOK_RESCAN);

	RunMacro(dir, i, tokenarray, buffer, 0, &is_exitm);
	Token_Count = i - 1;
	DebugMsg(("write_userdef_prologue: macro %s returned >%s<\n", ModuleInfo.proc_prologue, buffer));

	if (Parse_Pass == PASS_1) {
		struct dsym *curr;
		len = atoi(buffer) - info->localsize;
		for (curr = info->locallist; curr; curr = curr->nextlocal) {
			curr->sym.offset -= len;
		}
	}

	return (NOT_ERROR);
}

#if AMD64_SUPPORT

/* ========================================================================================================= */
/* OPTION WIN64:1 - save up to 4 register parameters for WIN64 fastcall */
/* ========================================================================================================= */
static void win64_SaveRegParams_RSP(struct proc_info *info)
/*******************************************************/
{
	int i;
	struct dsym *param;
	if (ModuleInfo.win64_flags & W64F_SMART) {
		uint_16        *regist;
		info->home_taken = 0;
		memset(info->home_used, 0, 6);
		if (info->regslist)
			regist = info->regslist;
		if (CurrProc->sym.langtype == LANG_VECTORCALL) {
			for (i = 0, param = info->paralist; param && (i < 6); i++) {
				/* v2.05: save XMMx if type is float/double */
				if (param->sym.is_vararg == FALSE) {
					if ((param->sym.mem_type & MT_FLOAT) && param->sym.used) {
						if (param->sym.mem_type == MT_REAL8)
							AddLineQueueX("%s qword ptr[%r+%u], %r", MOVE_DOUBLE(), T_RSP, 8 + i * 8, T_XMM0 + i);
						else if (param->sym.mem_type == MT_REAL4)
							AddLineQueueX("%s dword ptr[%r+%u], %r", MOVE_SINGLE(), T_RSP, 8 + i * 8, T_XMM0 + i);
						info->home_used[i] = 1;
						++info->home_taken;
					}
					else if ((param->sym.mem_type == MT_TYPE) && param->sym.used)
					{
						info->home_used[i] = 1;
						++info->home_taken;
						info->vecused = TRUE;
					}
					else {
						if (((param->sym.mem_type != MT_TYPE) && param->sym.used) &&
							(param->sym.mem_type <= MT_QWORD) && param->sym.used) {
							if (i < 4) {
								AddLineQueueX("mov [%r+%u], %r", T_RSP, 8 + i * 8, ms64_regs[i]);
								info->home_used[i] = 1;
								++info->home_taken;
							}
						}
					}
					param = param->nextparam;
				}
				else { /* v2.09: else branch added */
					AddLineQueueX("mov [%r+%u], %r", T_RSP, 8 + i * 8, ms64_regs[i]);
					info->home_used[i] = 1;
					++info->home_taken;
				}
			}
		}
		else {
			for (i = 0, param = info->paralist; param && (i < 4); i++) {
				/* v2.05: save XMMx if type is float/double */
				if (param->sym.is_vararg == FALSE) {
					if (param->sym.mem_type & MT_FLOAT && param->sym.total_size == 10) {
						/* UASM 2.52 emit a warning for trying to pass an REAL10 by value - don't want to be caught out expecting a value instead of ref */
						if (Parse_Pass == PASS_1) 
							EmitWarn(2, REAL10_BY_VALUE);
					}
					if (param->sym.mem_type & MT_FLOAT && param->sym.total_size == 4 && param->sym.used) {
						AddLineQueueX("%s [%r+%u], %r", MOVE_SIMD_DWORD(), T_RSP, 8 + i * 8, T_XMM0 + i);
						info->home_used[i] = 1;
						++info->home_taken;
					}
					else if (param->sym.mem_type & MT_FLOAT && param->sym.total_size == 8 && param->sym.used) {
						AddLineQueueX("%s [%r+%u], %r", MOVE_SIMD_QWORD(), T_RSP, 8 + i * 8, T_XMM0 + i);
						info->home_used[i] = 1;
						++info->home_taken;
					}
					else {
						if (param->sym.used) {                                    //here as well 
							AddLineQueueX("mov [%r+%u], %r", T_RSP, 8 + i * 8, ms64_regs[i]);
							info->home_used[i] = 1;
							++info->home_taken;
						}
					}
					param = param->nextparam;
				}
				else { /* v2.09: else branch added */
					AddLineQueueX("mov [%r+%u], %r", T_RSP, 8 + i * 8, ms64_regs[i]);
					info->home_used[i] = 1;
					++info->home_taken;
				}
			}
		}
	}
	else {
		for (i = 0, param = info->paralist; param && (i < 4); i++) {
			/* v2.05: save XMMx if type is float/double */
			if (param->sym.is_vararg == FALSE) {
				if (param->sym.mem_type & MT_FLOAT)
					AddLineQueueX("%s [%r+%u], %r", MOVE_SIMD_QWORD(), T_RSP, 8 + i * 8, T_XMM0 + i);
				else
					AddLineQueueX("mov [%r+%u], %r", T_RSP, 8 + i * 8, ms64_regs[i]);
				param = param->nextparam;
			}
			else { /* v2.09: else branch added */
				AddLineQueueX("mov [%r+%u], %r", T_RSP, 8 + i * 8, ms64_regs[i]);
			}
		}
	}
	return;
}

/* ========================================================================================================= */
/* WIN64 Store USED registers into free shadow spaces                                                        */
/* ========================================================================================================= */
static void win64_StoreRegHome(struct proc_info *info)
/*******************************************************/
{
	int			       i = 0;
	int			       cnt;
	int            grcount = 0;
	int			       sizestd = 0;
	int            freeshadow = 4;
	uint_16        *regist;
	info->stored_reg = 0;
	if (info->regslist) {
		for (regist = info->regslist, cnt = *regist++; cnt; cnt--, regist++, i++) {
			if ((GetValueSp(*regist) & OP_YMM) || (GetValueSp(*regist) & OP_XMM) || (GetValueSp(*regist) & OP_ZMM))
				continue;
			else ++grcount;                                       //find how many general registers to save
		}
		//for (i = 0, freeshadow = 0; i<4; i++){                  
		//  if (info->home_used[i] == 0) ++freeshadow;
		//}
		freeshadow -= info->home_taken;                         //find out how many free shadows
		if (freeshadow) {                                        //skip if all shadow spaces are taken  
			if (grcount == 1) memset(info->home_used, 1, 4);      //1 register only? don't store it, push it to prevent 'sub rsp,...8'
			else if (grcount == 2 && freeshadow >= 2) {            //store only one egister, another push to prevent 'sub rsp,...8'
				for (i = 0; i<4; i++) {
					if (info->home_used[i] == 0) break;               //we need only one space   
				}
				for (++i; i<4; i++)                                 //the rest of free spaces render as taken
					info->home_used[i] = 1;
			}
			else if (grcount == 3) {                               //3 registers?
				if (freeshadow == 1) memset(info->home_used, 1, 4); //if only 1 free shadow, don't store it, push them
				if (freeshadow >= 3) {                               //enen if there is enough space we will store only two
					for (i = 0; i<4; i++) {                            //the third one we will push to keep uneven stack 
						if (info->home_used[i] == 0) break;             //found first availible
					}
					for (++i; i<4; i++) {
						if (info->home_used[i] == 0) break;            //found second availible
					}
					for (++i; i<4; i++)
						info->home_used[i] = 1;                        //render the rest of the shadow spaces as taken
				}
			}
			else if (grcount == 4 && freeshadow == 4) {          //easy case
				info->home_used[3] = 1;                           //render the last shadow spaces as taken
			}                                                   //remember the first space is 0 than 1, 2 and 3 follow 
			else if (grcount > 4) {                              //if more registars than spaces
				freeshadow = grcount - freeshadow;                //find out how many we can store
				if (!(freeshadow & 1)) {                           //if it is even number
					for (i = 0; i<4; i++) {                          //than we have to disable one space
						if (info->home_used[i] == 0) break;           //find the first free space 
					}
					info->home_used[i] = 1;                         //and render it as taken
				}
			}
		}
		for (i = 0, regist = info->regslist, cnt = *regist++; cnt; cnt--, regist++, i++) {
			if ((GetValueSp(*regist) & OP_YMM) || (GetValueSp(*regist) & OP_XMM) || (GetValueSp(*regist) & OP_ZMM)) {
				i--;
				continue;
			}
			else {
				sizestd += 8;
				if (i < 4)
				{
					if (info->home_used[i] == 0) {
						AddLineQueueX("mov [%r+%u], %r", T_RSP, NUMQUAL sizestd, *regist);
						AddLineQueueX("%r %r, %u", T_DOT_SAVEREG, *regist, NUMQUAL sizestd);
						info->stored_reg++;
					}
					else {
						cnt++; regist--;
					}
				}
			}
		}/* end for */
	}
	return;
}

/* ========================================================================================================= */
/* WIN64 Return a correctly sized sub register from a 64bit fastcall parameter register                      */
/* ========================================================================================================= */
static enum special_token GetWin64SubReg(enum special_token srcReg,int type)
{
	if (type == 0)
	{
		if (srcReg == T_RCX)
			return(T_CL);
		if (srcReg == T_RDX)
			return(T_DL);
		if (srcReg == T_R8)
			return(T_R8B);
		if (srcReg == T_R9)
			return(T_R9B);
	}
	else if (type == 1)
	{
		if (srcReg == T_RCX)
			return(T_CX);
		if (srcReg == T_RDX)
			return(T_DX);
		if (srcReg == T_R8)
			return(T_R8W);
		if (srcReg == T_R9)
			return(T_R9W);
	}
	else if (type == 2)
	{
		if (srcReg == T_RCX)
			return(T_ECX);
		if (srcReg == T_RDX)
			return(T_EDX);
		if (srcReg == T_R8)
			return(T_R8D);
		if (srcReg == T_R9)
			return(T_R9D);
	}
	return(srcReg);
}

/* ========================================================================================================= */
/* OPTION WIN64:1 - save up to 4 register parameters for WIN64 fastcall                                      */
/* ========================================================================================================= */
static int win64_SaveRegParams_RBP(struct proc_info *info)
/*******************************************************/
{
	int i;
	struct dsym *param;
	int saved = 0;
	for (i = 0, param = info->paralist; param && (i < 4); i++)
	{
		/* v2.05: save XMMx if type is float/double */
		if (param->sym.is_vararg == FALSE)
		{
			if (param->sym.mem_type & MT_FLOAT && param->sym.total_size == 4 && param->sym.used) {
				AddLineQueueX("%s [%r+%u], %r", MOVE_SINGLE(), T_RSP, 8 + i * 8, T_XMM0 + i);
				saved++;
			}
			else if (param->sym.mem_type & MT_FLOAT && param->sym.total_size == 8 && param->sym.used) {
				AddLineQueueX("%s [%r+%u], %r", MOVE_DOUBLE(), T_RSP, 8 + i * 8, T_XMM0 + i);
				saved++;
			}
			else if (param->sym.used)
			{
				if (param->sym.mem_type == MT_BYTE || param->sym.mem_type == MT_SBYTE) {
					AddLineQueueX("mov [%r+%u], %r", T_RSP, 8 + i * 8, GetWin64SubReg(ms64_regs[i], 0));
					saved++;
				}
				else if (param->sym.mem_type == MT_WORD || param->sym.mem_type == MT_SWORD) {
					AddLineQueueX("mov [%r+%u], %r", T_RSP, 8 + i * 8, GetWin64SubReg(ms64_regs[i], 1));
					saved++;
				}
				else if (param->sym.mem_type == MT_DWORD || param->sym.mem_type == MT_SDWORD) {
					AddLineQueueX("mov [%r+%u], %r", T_RSP, 8 + i * 8, GetWin64SubReg(ms64_regs[i], 2));
					saved++;
				}
				else {
					AddLineQueueX("mov [%r+%u], %r", T_RSP, 8 + i * 8, ms64_regs[i]);
					saved++;
				}
			}
			param = param->nextparam;
		}
		else 
		{ 
			AddLineQueueX("mov [%r+%u], %r", T_RSP, 8 + i * 8, ms64_regs[i]);
			saved++;
		}
	}
	return saved;
}

/* ========================================================================================================= */
/* win64 default prologue when PROC FRAME and OPTION FRAME:AUTO is set                                       */
/* ========================================================================================================= */
static void write_win64_default_prologue_RBP(struct proc_info *info)
/****************************************************************/
{
	uint_16             *regist;
	const char * const  *ppfmt;
	int                 i;
	int                 cnt;
	int                 cntxmm;
	int                 resstack = ((ModuleInfo.win64_flags & W64F_AUTOSTACKSP) ? sym_ReservedStack->value : 0);
	int                 stackadj = 0;
	int                 subAmt = 0;
	int                 saved = 0;

	check_proc_fpo(info);
	
	info->pushed_reg = 0;

	if (ModuleInfo.win64_flags & W64F_SAVEREGPARAMS)
		saved = win64_SaveRegParams_RBP(info);

	/*
	* DB 48h
	* PUSH RBP
	* .PUSHREG RBP
	*/
	if ((info->isframe && ModuleInfo.frame_auto) || !info->isframe)
	{
		if (info->fpo)
		{
			/* do nothing */
		}
		else if (!info->fpo || info->forceframe)
		{
			if (info->isframe && ModuleInfo.frame_auto && saved == 0)
				AddLineQueueX("db 48h"); //Add this for hot patching - UASM 2.57, only add rex prefix if first instr.
			AddLineQueueX("push %r", info->basereg);
			if (info->isframe && ModuleInfo.frame_auto)
				AddLineQueueX("%r %r", T_DOT_PUSHREG, info->basereg);
		}
	
		/* Save the non-volatile registers */
		cntxmm = 0;
		if (info->regslist) {
			regist = info->regslist;
			for (cnt = *regist++; cnt; cnt--, regist++) {
				/* AVX registers will be multiplied with their correct size; 2.26 */
				if (GetValueSp(*regist) & OP_XMM) {
					cntxmm += 1;                         // 1 * 16
				}
				else if (GetValueSp(*regist) & OP_YMM) {
					cntxmm += 2;                         // 2 * 16
				}
				else if (GetValueSp(*regist) & OP_ZMM) {
					cntxmm += 4;                         // 4 * 16
				}
				else {
					info->pushed_reg += 1;
					AddLineQueueX("push %r", *regist);
					if ((1 << GetRegNo(*regist)) & win64_nvgpr) {
						if (info->isframe && ModuleInfo.frame_auto)
							AddLineQueueX("%r %r", T_DOT_PUSHREG, *regist);
					}
				}
			} /* end for */
		}
	}

	/* Only allow uses xmm's with frame procs */
	if (!info->isframe && cntxmm > 0)
	{
		EmitError(PROC_USES_XMM);
		return;
	}

	/* adjust stack to be 16byte aligned if required */
	/* or at least account for odd pushed gprs */
	if (ModuleInfo.win64_flags & W64F_STACKALIGN16 || ModuleInfo.win64_flags & W64F_AUTOSTACKSP || ModuleInfo.frame_auto)
	{
		if (info->fpo)
		{
			if (info->pushed_reg % 2 == 0 && info->localsize % 16 == 0)
				stackadj = 8;
			else if (info->pushed_reg % 2 == 0 && info->localsize % 16 != 0)
				stackadj = 0;
			else if (info->pushed_reg % 2 != 0 && info->localsize % 16 == 0)
				stackadj = 0;
			else if (info->pushed_reg % 2 != 0 && info->localsize % 16 != 0)
				stackadj = 8;
		}
		else
		{
			if (info->pushed_reg % 2 == 0 && info->localsize % 16 == 0)
				stackadj = 0;
			else if (info->pushed_reg % 2 == 0 && info->localsize % 16 != 0)
				stackadj = 8;
			else if (info->pushed_reg % 2 != 0 && info->localsize % 16 == 0)
				stackadj = 8;
			else if (info->pushed_reg % 2 != 0 && info->localsize % 16 != 0)
				stackadj = 0;
		}
	}

	if ((info->isframe && ModuleInfo.frame_auto) || !info->isframe)
	{
		if (!info->fpo || info->stackparam || info->has_vararg || ModuleInfo.win64_flags & W64F_STACKALIGN16 || ModuleInfo.win64_flags & W64F_AUTOSTACKSP)
		{
			DebugMsg1(("write_win64_default_prologue_RBP: localsize=%u resstack=%u\n", info->localsize, resstack));
			/*
			* SUB  RSP, localsize
			* .ALLOCSTACK localsize
			*/
			ppfmt = (resstack ? fmtstk1 : fmtstk0);
			#if STACKPROBE
			if (info->localsize + stackadj + resstack > 0x1000) {
				AddLineQueueX(*(ppfmt + 2), T_RAX, NUMQUAL info->localsize + stackadj, sym_ReservedStack->name);
				AddLineQueue("externdef __chkstk:PROC");
				AddLineQueue("call __chkstk");
				AddLineQueueX("mov %r, %r", T_RSP, T_RAX);
			}
			else
			#endif
			if (info->localsize + stackadj + resstack > 0)
			{
				subAmt = info->localsize + stackadj + sym_ReservedStack->value;
				
				if (Options.frameflags)
				{
					if (resstack)
						AddLineQueueX("lea %r, [%r-(%d+%s)]", T_RSP, T_RSP, NUMQUAL info->localsize + stackadj, sym_ReservedStack->name);
					else
						AddLineQueueX("lea %r, [%r-%d]", T_RSP, T_RSP, NUMQUAL info->localsize + stackadj, sym_ReservedStack->name);
				}
				else
				{
					AddLineQueueX(*(ppfmt + 0), T_RSP, NUMQUAL info->localsize + stackadj, sym_ReservedStack->name);
				}

				if (info->isframe && ModuleInfo.frame_auto)
					AddLineQueueX(*(ppfmt + 1), T_DOT_ALLOCSTACK, NUMQUAL info->localsize + stackadj, sym_ReservedStack->name);
			}
		}
		else if (stackadj + info->localsize > 0 && ModuleInfo.frame_auto)
		{
			subAmt = info->localsize + stackadj;

			if (Options.frameflags)
			{
				AddLineQueueX("lea %r, [%r-%d]", T_RSP, T_RSP, NUMQUAL stackadj + info->localsize);
			}
			else
			{
				AddLineQueueX("sub %r, %d", T_RSP, NUMQUAL stackadj + info->localsize);
			}

			if (info->isframe && ModuleInfo.frame_auto)
				AddLineQueueX("%r %d", T_DOT_ALLOCSTACK, NUMQUAL stackadj + info->localsize);
		}
	}

	/* save xmm registers */
	if (cntxmm) {
		regist = info->regslist;
		/* firs location must be multiplied by 16 and subtracted
		*  from info->localsize and aligned to 16  ; Uasm 2.26 */
		i = (info->localsize - cntxmm * 16) & ~(16 - 1);
		if (regist) {
			for (cnt = *regist++; cnt; cnt--, regist++) {
				if (resstack) {                         //sym_ReservedStack has value
					if (GetValueSp(*regist) & OP_XMM) {
						AddLineQueueX("%s [%r+%u+%s], %r", MOVE_ALIGNED_INT(), T_RSP, NUMQUAL i, sym_ReservedStack->name, *regist);
						if (info->isframe && ModuleInfo.frame_auto)
							AddLineQueueX("%r %r, %u+%s", T_DOT_SAVEXMM128, *regist, NUMQUAL i, sym_ReservedStack->name);
						i += 16;
					}
					else if (GetValueSp(*regist) & OP_YMM) {
						AddLineQueueX("%s [%r+%u+%s], %r", MOVE_UNALIGNED_INT(), T_RSP, NUMQUAL i, sym_ReservedStack->name, *regist);
						if (info->isframe && ModuleInfo.frame_auto)
							AddLineQueueX("%r %r, %u+%s", T_DOT_SAVEYMM256, *regist, NUMQUAL i, sym_ReservedStack->name);
						i += 32;
					}
					else if (GetValueSp(*regist) & OP_ZMM) {
						AddLineQueueX("%s [%r+%u+%s], %r", MOVE_UNALIGNED_INT(), T_RSP, NUMQUAL i, sym_ReservedStack->name, *regist);
						if (info->isframe && ModuleInfo.frame_auto)
							AddLineQueueX("%r %r, %u+%s", T_DOT_SAVEZMM512, *regist, NUMQUAL i, sym_ReservedStack->name);
						i += 64;
					}
				}
				else {                                   // sym_ReservedStack has no value
					if (GetValueSp(*regist) & OP_XMM) {
						AddLineQueueX("%s [%r+%u], %r", MOVE_ALIGNED_INT(), T_RSP, NUMQUAL i, *regist);
						if (info->isframe && ModuleInfo.frame_auto)
							AddLineQueueX("%r %r, %u", T_DOT_SAVEXMM128, *regist, NUMQUAL i);
						i += 16;
					}
					else if (GetValueSp(*regist) & OP_YMM) {
						AddLineQueueX("%s [%r+%u], %r", MOVE_UNALIGNED_INT(), T_RSP, NUMQUAL i, *regist);
						if (info->isframe && ModuleInfo.frame_auto)
							AddLineQueueX("%r %r, %u", T_DOT_SAVEYMM256, *regist, NUMQUAL i);
						i += 32;
					}
					else if (GetValueSp(*regist) & OP_ZMM) {
						AddLineQueueX("%s [%r+%u+%s], %r", MOVE_UNALIGNED_INT(), T_RSP, NUMQUAL i, *regist);
						if (info->isframe && ModuleInfo.frame_auto)
							AddLineQueueX("%r %r, %u+%s", T_DOT_SAVEZMM512, *regist, NUMQUAL i);
						i += 64;
					}
				}
			}
		}
	}

	/*
	* MOV RBP, RSP
	* .SETFRAME RBP, 0
	*/
	if ((info->isframe && ModuleInfo.frame_auto) || !info->isframe)
	{
		if (info->fpo)
		{
			/* do nothing */
		}
		else if (!info->fpo || info->forceframe)
		{
			if (info->frameofs != 0)
				AddLineQueueX("lea %r, [%r + %d]", info->basereg, T_RSP, info->frameofs);
			else
				AddLineQueueX("mov %r, %r", info->basereg, T_RSP);

			if (info->isframe && ModuleInfo.frame_auto)
				AddLineQueueX( "%r %r, %d", T_DOT_SETFRAME, info->basereg, info->frameofs );
		}

		if (info->isframe && ModuleInfo.frame_auto)
			AddLineQueueX("%r", T_DOT_ENDPROLOG);
	}
	return;
}

/* ========================================================================================================= */
/* win64 default prologue when PROC FRAME and  OPTION FRAME:AUTO is set                                      */
/* ========================================================================================================= */
static void write_win64_default_prologue_RSP(struct proc_info *info)
/****************************************************************/
{
	uint_16             *regist;
	const char * const  *ppfmt;
	int                 cntxmm;
	unsigned char xyused[6];  /* flags for used sse registers in vectorcall */
	unsigned char       xreg;
	unsigned char       xsize;
	unsigned char       ymmflag = 0;
	unsigned char       zmmflag = 0;
	int                 vsize = 0;
	int                 vectstart = 0;
	int                 n;
	int                 m;
	int                 i;
	int                 j;
	int                 cnt;
	int                 stackSize;
	int                 resstack = ((ModuleInfo.win64_flags & W64F_AUTOSTACKSP) ? sym_ReservedStack->value : 0);
	int pushed = 0;

	if (Parse_Pass == PASS_1)
	{
		info->vsize = 0;
		info->xmmsize = 0;
	}

	memset(xyused, 0, 6);
	info->vecused = 0;
	XYZMMsize = 16;

	if (ModuleInfo.win64_flags & W64F_SAVEREGPARAMS)
		win64_SaveRegParams_RSP(info);

	if (ModuleInfo.win64_flags & W64F_SMART)
		win64_StoreRegHome(info);

#if STACKBASESUPP

	info->pushed_reg = 0; /*count of pushed registers */
	if (info->regslist != 0)
		pushed = *(info->regslist);

#endif

	//if (ModuleInfo.win64_flags & W64F_SMART)
	//{
		cntxmm = 0;
		if (info->regslist) {
			n = 0;
			regist = info->regslist;
			for (cnt = *regist++; cnt; cnt--, regist++) {
				if (GetValueSp(*regist) & OP_XMM) {
					cntxmm += 1;
				}
				else if (GetValueSp(*regist) & OP_YMM) {
					cntxmm += 1;
					ymmflag = 1;
				}
				else if (GetValueSp(*regist) & OP_ZMM) {
					cntxmm += 1;
					zmmflag = 1;
				}
				else {
					if (n < info->stored_reg) n++;
					else {
						info->pushed_reg += 1;
						AddLineQueueX("push %r", *regist);
						if ((1 << GetRegNo(*regist)) & win64_nvgpr) {
							AddLineQueueX("%r %r", T_DOT_PUSHREG, *regist);
						}
					}
				}
			} /* end for */
		}
	//}

	if (zmmflag) XYZMMsize = 64;
	else
		if (ymmflag) XYZMMsize = 32;
		else XYZMMsize = 16;
		/* v2.11: now done in write_prologue() */
		if (ModuleInfo.win64_flags & W64F_HABRAN)
		{
			if (!(info->locallist) && !(resstack)) info->localsize = 0;
			if ((info->localsize == 0) && (cntxmm))
			{
				CurrProc->e.procinfo->xmmsize = cntxmm * XYZMMsize;
				if ((info->pushed_reg & 1) == 0)
					info->localsize = 8;
			}
		}

		if ((info->locallist + resstack) || info->vecused || CurrProc->e.procinfo->xmmsize) {
			DebugMsg1(("write_win64_default_prologue_RSP: localsize=%u resstack=%u\n", info->localsize, resstack));
			if (ModuleInfo.win64_flags & W64F_HABRAN) {
				if (((info->pushed_reg & 1) && (info->localsize & 0xF)) ||
					((!(info->pushed_reg & 1)) && (!(info->localsize & 0xF))) && (!(info->pushed_reg & 1)) && (!(cntxmm)))
				{
					info->localsize += 8;
					if (CurrProc->sym.langtype == LANG_VECTORCALL) {
						vectstart = 0;
					}
				}
			}
			/*
			* SUB  RSP, localsize
			* .ALLOCSTACK localsize
			*/

			ppfmt = (resstack ? fmtstk1 : fmtstk0);
#if STACKPROBE
			if (info->localsize + resstack > 0x1000) {
				AddLineQueueX(*(ppfmt + 2), T_RAX, NUMQUAL info->localsize, sym_ReservedStack->name);
				AddLineQueue("externdef __chkstk:PROC");
				AddLineQueue("call __chkstk");
				AddLineQueueX("mov %r, %r", T_RSP, T_RAX);
			}
			else
#endif
				stackSize = info->localsize + info->vsize + info->xmmsize;
			if ((stackSize & 7) != 0) stackSize = (stackSize + 7)&(-8);

			if (Options.frameflags)
			{
				if(resstack)
					AddLineQueueX("lea %r, [%r-(%d+%s)]", T_RSP, T_RSP, NUMQUAL stackSize, sym_ReservedStack->name);
				else
					AddLineQueueX("lea %r, [%r-%d]", T_RSP, T_RSP, NUMQUAL stackSize, sym_ReservedStack->name);
			}
			else
			{
				AddLineQueueX(*(ppfmt + 0), T_RSP, NUMQUAL stackSize, sym_ReservedStack->name);
			}
			AddLineQueueX(*(ppfmt + 1), T_DOT_ALLOCSTACK, NUMQUAL stackSize, sym_ReservedStack->name);

			/* save xmm registers */
			if (cntxmm) {
				int cnt;
				regist = info->regslist;
				i = 0;       //firs location is right at the [rsp+32] which is aligned to 16  ; Uasm 2.21
				if (regist)
				{
					for (cnt = *regist++; cnt; cnt--, regist++)
					{
						if ((GetValueSp(*regist) & OP_XMM) || (GetValueSp(*regist) & OP_YMM) || (GetValueSp(*regist) & OP_ZMM)) {
							if (resstack) {
								//if ( ( 1 << GetRegNo( *regist ) ) & win64_nvxmm )  {
								if (GetValueSp(*regist) & OP_XMM) {
									AddLineQueueX("%s [%r+%u+%s], %r", MOVE_ALIGNED_INT(), T_RSP, NUMQUAL i, sym_ReservedStack->name, *regist);
									AddLineQueueX("%r %r, %u+%s", T_DOT_SAVEXMM128, *regist, NUMQUAL i, sym_ReservedStack->name);
									i += 16;// XYZMMsize;
								}
								else if (GetValueSp(*regist) & OP_YMM) {
									AddLineQueueX("vmovdqu [%r+%u+%s], %r", T_RSP, NUMQUAL i, sym_ReservedStack->name, *regist);
									AddLineQueueX("%r %r, %u+%s", T_DOT_SAVEYMM256, *regist, NUMQUAL i, sym_ReservedStack->name);
									i += 32;// XYZMMsize;
								}
								else if (GetValueSp(*regist) & OP_ZMM) {
									AddLineQueueX("vmovdqu [%r+%u+%s], %r", T_RSP, NUMQUAL i, sym_ReservedStack->name, *regist);
									AddLineQueueX("%r %r, %u+%s", T_DOT_SAVEZMM512, *regist, NUMQUAL i, sym_ReservedStack->name);
									i += 64;// XYZMMsize;
								}
								// }
							}
							else {
								// if ( ( 1 << GetRegNo( *regist ) ) & win64_nvxmm )  {
								if (GetValueSp(*regist) & OP_XMM) {
									AddLineQueueX("%s [%r+%u], %r", MOVE_ALIGNED_INT(), T_RSP, NUMQUAL i, *regist);
									AddLineQueueX("%r %r, %u", T_DOT_SAVEXMM128, *regist, NUMQUAL i);
									i += 16;// XYZMMsize;
								}
								else if (GetValueSp(*regist) & OP_YMM) {
									AddLineQueueX("vmovdqu [%r+%u], %r", T_RSP, NUMQUAL i, *regist);
									AddLineQueueX("%r %r, %u", T_DOT_SAVEYMM256, *regist, NUMQUAL i);
									i += 32;// XYZMMsize;
								}
								else if (GetValueSp(*regist) & OP_ZMM) {
									AddLineQueueX("vmovdqu [%r+%u+%s], %r", T_RSP, NUMQUAL i, *regist);
									AddLineQueueX("%r %r, %u+%s", T_DOT_SAVEZMM512, *regist, NUMQUAL i);
									i += 64;// XYZMMsize;
								}
								// }
							}
						}
					}
				}
			}
			/* For VECTORCALL save vectors in the space provided */
			if (CurrProc->sym.langtype == LANG_VECTORCALL) {
				vectstart = info->localsize + info->xmmsize & ~(16 - 1);
				if (info->vecused) {
					if (info->vecregs) {
						for (n = 0, m = 0, xsize = 0; n < 6; n++) {
							xreg = info->vecregs[n];
							if (xreg == 1 && info->vecregsize[n] < 16)
								continue;//REAL4, FLOAT and REAL8 are stored in homespace
							else if (xreg)
							{
								AddLineQueueX("lea %r,[%r + %d]", T_RAX, T_RSP, vectstart + xsize);
								stackSize = info->localsize + resstack + info->vsize + info->xmmsize + 8 + info->pushed_reg * 8 + n * 8;
								if ((stackSize & 7) != 0) stackSize = (stackSize + 7)&(-8);
								AddLineQueueX("mov [%r + %d], %r", T_RSP, stackSize, T_RAX);
								xsize += info->vecregsize[n] * xreg;
							}
							else if (info->vregs[n] != 0 && xreg == 0 && n < 4) /* JPH */
							{
								struct dsym *pp = info->paralist;
								int j = 0;
								for (j = 0; j < n; j++)
								{
									if (pp) pp = pp->nextparam;
								}
								if (pp)
								{
									if (pp->sym.ttype)
									{
										if (pp->sym.ttype->e.structinfo->isHFA == 1 || pp->sym.ttype->e.structinfo->isHVA == 1 || pp->sym.ttype->e.structinfo->stype == MM128 || pp->sym.ttype->e.structinfo->stype == MM256)
										{
											stackSize = info->localsize + resstack + info->vsize + info->xmmsize + 8 + info->pushed_reg * 8 + n * 8;
											if ((stackSize & 7) != 0) stackSize = (stackSize + 7)&(-8);
											AddLineQueueX("mov [%r + %d], %r", T_RSP, stackSize, ms64_regs[n]);
											//xsize += 8;
											xsize += info->vecregsize[n] * xreg;
										}
									}
								}
							}
						}
						/* set available registers to zero including the ones that are greater than 1 */
						for (i = 0; i < 6; i++) {
							if (info->vecregs[i] == 1) xyused[i] = 1;
							else if ((info->vecregs[i] >= 1) && (xyused[i] != 1))
								xyused[i] = 0;
						}
						for (n = 0, m = 0; n < 6; n++) {
							xreg = info->vecregs[n];       // it can be 0, 1, 2 or 4 eg: 0, 4, 0, 2, 0, 0
							xsize = info->vecregsize[n];   // xmm = 16, ymm = 32 or zmm = 64
							m += xreg;
							if (m > 6) break;              // max 6 AVX registers
							if (xreg == 1 && info->vecregsize[n] < 16)
								continue;                    //REAL4, FLOAT and REAL8 are stored in homespace
							else if (xreg) {
								switch (xsize) {
								case 4:
									//if (xreg == 2){
									//  /* this can only happen if there is 2 real4 */
									//  AddLineQueueX("vmovsd qword ptr [rsp+%d],%r", vsize + vectstart, T_XMM0 + n);
									//  vsize += 8;
									//  }
									//else{
									for (i = 0, j = 0; i < xreg; i++) {
										while (xyused[j] != 0) j++;
										AddLineQueueX("%s dword ptr [rsp+%d],%r", MOVE_SINGLE(), vsize + vectstart, T_XMM0 + j);
										xyused[j] = 1;
										vsize += 4;
									}
									//}
									break;
								case 8:
									if (xreg <= 3) {
										for (i = 0, j = 0; i < xreg; i++) {
											while (xyused[j] != 0) j++;
											AddLineQueueX("%s qword ptr [rsp+%d],%r", MOVE_DOUBLE(), vsize + vectstart, T_XMM0 + j);
											xyused[j] = 1;
											vsize += 8;
										}
									}
									/* this can only happen if there is 8 real8 */
									else {
										AddLineQueueX("vmovups ymmword ptr [rsp+%d],%r", vsize + vectstart, T_YMM0 + n);
										vsize += 64;
										xyused[n] = 1;
									}
									break;
								case 16:
									if (xreg == 1) {
										AddLineQueueX("%s oword ptr [rsp+%d],%r", MOVE_UNALIGNED_FLOAT(), vsize + vectstart, T_XMM0 + n);
										xyused[n] = 1;
										vsize += 16;
									}
									else {
										for (i = 0, j = 0; i < xreg; i++) {
											while (xyused[j] != 0) j++;
											AddLineQueueX("%s oword ptr [rsp+%d],%r", MOVE_UNALIGNED_FLOAT(), vsize + vectstart, T_XMM0 + j);
											xyused[j] = 1;
											vsize += 16;
										}
									}
									break;
								case 32:
									if (xreg == 1) {
										AddLineQueueX("vmovups ymmword ptr [rsp+%d],%r", vsize + vectstart, T_YMM0 + n);
										xyused[n] = 1;
										vsize += 32;
									}
									else {
										for (i = 0, j = 0; i < xreg; i++) {
											while (xyused[j] != 0) j++;
											AddLineQueueX("vmovups ymmword ptr [rsp+%d],%r", vsize + vectstart, T_YMM0 + j);
											xyused[j] = 1;
											vsize += 32;
										}
									}
									break;
								case 64:
									if (xreg == 1) {
										AddLineQueueX("vmovups zmmword ptr [rsp+%d],%r", vsize + vectstart + xsize, T_ZMM0 + n);
										xyused[n] = 1;
										vsize += 64;
									}
									else {
										for (i = 0, j = 0; i < xreg; i++) {
											while (xyused[j] != 0) j++;
											AddLineQueueX("vmovups zmmword ptr [rsp+%d],%r", vsize + vectstart + xsize, T_ZMM0 + j);
											xyused[j] = 1;
											vsize += 64;
										}
									}
									break;
								}
							}
						}
					}
				}
			}
		}
		else if (info->localsize > 0)
		{
			stackSize = info->localsize;
			if (Options.frameflags)
			{
				AddLineQueueX("lea %r, [%r-%d]", stackreg[ModuleInfo.Ofssize], stackreg[ModuleInfo.Ofssize], stackSize);
			}
			else
			{
				AddLineQueueX("sub %r, %d", stackreg[ModuleInfo.Ofssize], stackSize);
			}
		}

		AddLineQueueX("%r", T_DOT_ENDPROLOG);

		/* v2.11: linequeue is now run in write_default_prologue() */
		return;
}

/* ========================================================================================================= */
/* Check to see if a proc can have FPO enabled                                                               */
/* ========================================================================================================= */
static void check_proc_fpo(struct proc_info *info)
{
	struct dsym *paracurr;
	int usedParams = 0;
	int usedLocals = 0;

	for (paracurr = info->paralist; paracurr; paracurr = paracurr->nextparam)
			usedParams++;
	for (paracurr = info->locallist; paracurr; paracurr = paracurr->nextlocal)
			usedLocals++;

	//if (info->pushed_reg > 0)
	//{
	//	info->fpo = FALSE;
	//	return;
	//}

	if (info->exc_handler && ModuleInfo.basereg[ModuleInfo.Ofssize] == T_RBP)
	{
		info->fpo = FALSE;
		return;
	}

	if (ModuleInfo.basereg[ModuleInfo.Ofssize] == T_RSP || ModuleInfo.basereg[ModuleInfo.Ofssize] == T_ESP)
	{
		info->fpo = TRUE;
		return;
	}
	if (info->forceframe == TRUE)
	{
		info->fpo = FALSE;
		return;
	}

	if (!ModuleInfo.frame_auto && info->isframe)
	{
		info->fpo = TRUE;
		return;
	}
	if (!info->isframe && (usedParams>0 || usedLocals>0))
	{
		info->fpo = FALSE;
		return;
	}

	if (usedLocals > 0 || usedParams > 0 || Parse_Pass == PASS_1)
	{
		info->fpo = FALSE;
		return;
	}

	if (usedLocals == 0 && usedParams == 0)
		info->fpo = TRUE;

	return;
}

/* ========================================================================================================= */
/* Win64 default epilogue if PROC FRAME and OPTION FRAME:AUTO is set for RBP stackbase                       */
/* UASM WIN64:N version																						 */
/* ========================================================================================================= */
static void write_win64_default_epilogue_RBP(struct proc_info *info)
/****************************************************************/
{
	int  resstack = ((ModuleInfo.win64_flags & W64F_AUTOSTACKSP) ? sym_ReservedStack->value : 0);
	int  stackadj = 0;
	const char * const  *ppfmt;
	uint_16 restoreReg;

	if (info->fpo)
	{
		if (info->pushed_reg % 2 == 0 && info->localsize % 16 == 0)
			stackadj = 8;
		else if (info->pushed_reg % 2 == 0 && info->localsize % 16 != 0)
			stackadj = 0;
		else if (info->pushed_reg % 2 != 0 && info->localsize % 16 == 0)
			stackadj = 0;
		else if (info->pushed_reg % 2 != 0 && info->localsize % 16 != 0)
			stackadj = 8;
	}
	else
	{
		if (info->pushed_reg % 2 == 0 && info->localsize % 16 == 0)
			stackadj = 0;
		else if (info->pushed_reg % 2 == 0 && info->localsize % 16 != 0)
			stackadj = 8;
		else if (info->pushed_reg % 2 != 0 && info->localsize % 16 == 0)
			stackadj = 8;
		else if (info->pushed_reg % 2 != 0 && info->localsize % 16 != 0)
			stackadj = 0;
	}

	/* restore non-volatile xmm registers */
	if ((info->isframe && ModuleInfo.frame_auto) || !info->isframe)
	{
		if (info->regslist)
		{
			uint_16 *regs;
			int cnt;
			int i;
			//int total = info->localsize + stackadj + sym_ReservedStack->name;
			/* v2.12: space for xmm saves is now included in localsize
			* so first thing to do is to count the xmm regs that were saved
			*/
			for (regs = info->regslist, cnt = *regs++, i = 0; cnt; cnt--, regs++)
				if (GetValueSp(*regs) & OP_XMM)
					i++;
				else if (GetValueSp(*regs) & OP_YMM)
					i += 2;
				else if (GetValueSp(*regs) & OP_ZMM)
					i += 4;

			if (i)
			{

				i = (info->localsize - i * 16) & ~(16 - 1);
				if (info->fpo)
					restoreReg = stackreg[ModuleInfo.Ofssize];
				else
					restoreReg = info->basereg;

				for (regs = info->regslist, cnt = *regs++; cnt; cnt--, regs++) {
					if (GetValueSp(*regs) & OP_XMM) {
						DebugMsg1(("write_win64_default_epilogue(%s): restore %s, offset=%d\n", CurrProc->sym.name, GetResWName(*regs, NULL), i));
						if (ModuleInfo.win64_flags & W64F_AUTOSTACKSP)
							AddLineQueueX("%s %r, [%r + %d + %s]", MOVE_ALIGNED_INT(), *regs, restoreReg, NUMQUAL i - info->frameofs, sym_ReservedStack->name);
						else
							AddLineQueueX("%s %r, [%r + %d]", MOVE_ALIGNED_INT(), *regs, restoreReg, NUMQUAL i - info->frameofs);
						i += 16;
					}
					if (GetValueSp(*regs) & OP_YMM) {
						DebugMsg1(("write_win64_default_epilogue(%s): restore %s, offset=%d\n", CurrProc->sym.name, GetResWName(*regs, NULL), i));
						if (ModuleInfo.win64_flags & W64F_AUTOSTACKSP)
							AddLineQueueX("%s %r, [%r + %d + %s]", MOVE_UNALIGNED_INT(), *regs, restoreReg, NUMQUAL i - info->frameofs, sym_ReservedStack->name);
						else
							AddLineQueueX("%s %r, [%r + %d]", MOVE_UNALIGNED_INT(), *regs, restoreReg, NUMQUAL i - info->frameofs);
						i += 32;
					}
					if (GetValueSp(*regs) & OP_ZMM) {
						DebugMsg1(("write_win64_default_epilogue(%s): restore %s, offset=%d\n", CurrProc->sym.name, GetResWName(*regs, NULL), i));
						if (ModuleInfo.win64_flags & W64F_AUTOSTACKSP)
							AddLineQueueX("%s %r, [%r + %d + %s]", MOVE_UNALIGNED_INT(), *regs, restoreReg, NUMQUAL i - info->frameofs, sym_ReservedStack->name);
						else
							AddLineQueueX("%s %r, [%r + %d]", MOVE_UNALIGNED_INT(), *regs, restoreReg, NUMQUAL i - info->frameofs);
						i += 64;
					}
				}
			}
		}
	}

	/*
	* RESTORE RSP from RBP
	*/
	if ( (info->isframe && ModuleInfo.frame_auto) || !info->isframe )
	{
		if (!info->fpo || info->stackparam || info->has_vararg || ModuleInfo.win64_flags & W64F_STACKALIGN16 || ModuleInfo.win64_flags & W64F_AUTOSTACKSP)
		{
			if (!info->fpo)
			{
				ppfmt = (resstack ? fmtstk3 : fmtstk2);
				if (info->localsize + stackadj + resstack > 0)
				{
					AddLineQueueX(*(ppfmt + 0), T_RSP, info->basereg, NUMQUAL stackadj + info->localsize - info->frameofs, sym_ReservedStack->name);
				}
				else
					AddLineQueueX("mov %r, %r", T_RSP, info->basereg);
			}

			// UASM 2.50 Modified by PR from db4.
			else if (info->localsize + stackadj + resstack > 0)
			{
				if (Options.frameflags)
				{
					AddLineQueueX("lea %r, [%r+(%d+%s)]", T_RSP, T_RSP, NUMQUAL stackadj + info->localsize, sym_ReservedStack->name);
				}
				else
				{
					AddLineQueueX("add %r, %d + %s", T_RSP, NUMQUAL stackadj + info->localsize, sym_ReservedStack->name);
				}
			}
		}
		else if (stackadj + info->localsize > 0 && ModuleInfo.frame_auto)
		{
			if (!info->fpo)
				AddLineQueueX("lea %r, [%r + %d]", T_RSP, info->basereg, NUMQUAL stackadj + info->localsize - info->frameofs);
			else
			{
				if (Options.frameflags)
				{
					AddLineQueueX("lea %r, [%r+%d]", T_RSP, T_RSP, NUMQUAL stackadj + info->localsize);
				}
				else
				{
					AddLineQueueX("add %r, %d", T_RSP, NUMQUAL stackadj + info->localsize);
				}
			}
		}

		pop_register(CurrProc->e.procinfo->regslist);
	
		if (!info->fpo)
			AddLineQueueX("pop %r", info->basereg);
	}
	return;
}

/* ========================================================================================================= */
/* Win64 default epilogue if PROC FRAME and OPTION FRAME:AUTO is set for stackbase RSP						 */
/* ========================================================================================================= */
static void write_win64_default_epilogue_RSP(struct proc_info *info)
/****************************************************************/
{
	int  anysize;
	int  stackSize;
	int  resstack = ((ModuleInfo.win64_flags & W64F_AUTOSTACKSP) ? sym_ReservedStack->value : 0);

	/* restore non-volatile xmm registers */
	if (info->regslist) {
		uint_16 *regs;
		int cnt;
		int i;


		/* v2.12: space for xmm saves is now included in localsize
		* so first thing to do is to count the xmm regs that were saved */
		for (regs = info->regslist, cnt = *regs++, i = 0; cnt; cnt--, regs++)
			if ((GetValueSp(*regs) & OP_XMM) || (GetValueSp(*regs) & OP_YMM) || (GetValueSp(*regs) & OP_ZMM))
				i++;
		DebugMsg1(("write_win64_default_epilogue_RSP(%s): %u xmm registers to restore\n", CurrProc->sym.name, i));
		if (i) {
			i = 0;       //firs location is right at the [rsp] which is aligned to 16 ; Uasm 2.21
			for (regs = info->regslist, cnt = *regs++; cnt; cnt--, regs++) {
				if ((GetValueSp(*regs) & OP_XMM) || (GetValueSp(*regs) & OP_YMM) || (GetValueSp(*regs) & OP_ZMM)) {
					DebugMsg1(("write_win64_default_epilogue_RSP(%s): restore %s, offset=%d\n", CurrProc->sym.name, GetResWName(*regs, NULL), i));
					/* v2.11: use @ReservedStack only if option win64:2 is set */
					if (resstack)
					{
						if (GetValueSp(*regs) & OP_XMM)
						{
							AddLineQueueX("%s %r, [%r + %u + %s]", MOVE_ALIGNED_INT(), *regs, stackreg[ModuleInfo.Ofssize], NUMQUAL i, sym_ReservedStack->name);
							i += 16;
						}
						else if (GetValueSp(*regs) & OP_YMM)
						{
							AddLineQueueX("vmovdqu %r, [%r + %u + %s]", *regs, stackreg[ModuleInfo.Ofssize], NUMQUAL i, sym_ReservedStack->name);
							i += 32;
						}
					}
					else
					{
						if (GetValueSp(*regs) & OP_XMM)
						{
							AddLineQueueX("%s %r, [%r + %u]", MOVE_ALIGNED_INT(), *regs, stackreg[ModuleInfo.Ofssize], NUMQUAL i);
							i += 16;
						}
						if (GetValueSp(*regs) & OP_YMM)
						{
							AddLineQueueX("vmovdqu %r, [%r + %u]", *regs, stackreg[ModuleInfo.Ofssize], NUMQUAL i);
							i += 32;
						}
					}
				}
			}
		}
	}

	if (ModuleInfo.fctype == FCT_WIN64 && (ModuleInfo.win64_flags & W64F_AUTOSTACKSP)) {
		anysize = info->localsize + sym_ReservedStack->value + info->xmmsize;
		if (info->vecused) anysize += info->vsize;
		if (anysize)
		{
			stackSize = info->localsize + info->vsize + info->xmmsize;
			if ((stackSize & 7) != 0) stackSize = (stackSize + 7)&(-8);
			
			if (Options.frameflags)
			{
				AddLineQueueX("lea %r, [%r+(%d+%s)]", stackreg[ModuleInfo.Ofssize], stackreg[ModuleInfo.Ofssize], NUMQUAL stackSize, sym_ReservedStack->name);
			}
			else
			{
				AddLineQueueX("add %r, %d + %s", stackreg[ModuleInfo.Ofssize], NUMQUAL stackSize, sym_ReservedStack->name);
			}
		}
	}
	else if (info->localsize > 0)
	{
		stackSize = info->localsize;
		if (Options.frameflags)
		{
			AddLineQueueX("lea %r, [%r+%d]", stackreg[ModuleInfo.Ofssize], stackreg[ModuleInfo.Ofssize], stackSize);
		}
		else
		{
			AddLineQueueX("add %r, %d", stackreg[ModuleInfo.Ofssize], stackSize);
		}
	}
	pop_register(CurrProc->e.procinfo->regslist); //make sure we pop before correcting RSP.

#if STACKBASESUPP
	if (ModuleInfo.win64_flags & W64F_SMART) {
		/* restore non-volatile registers from shadow space */
		if (info->regslist) {
			uint_16 *regist = info->regslist;
			int cnt;
			if (ModuleInfo.win64_flags) {
				int i = 0;
				int gprzize = 0;
				for (cnt = *regist++; cnt; cnt--, regist++)
				{
					if ((GetValueSp(*regist) & OP_XMM) || (GetValueSp(*regist) & OP_YMM) || (GetValueSp(*regist) & OP_ZMM))
						continue;
					else {
						gprzize += 8;
						if (gprzize <= 0x20)
						{
							if (info->home_used[i] == 0) {
								AddLineQueueX("mov %r, [%r+%u]", *regist, stackreg[ModuleInfo.Ofssize], NUMQUAL gprzize);
							}
							else {
								cnt++; regist--;
							}
							i++;
						}
					}
				}
			}
		}
	}
	if (GetRegNo(info->basereg) != 4 && (info->parasize != 0 || info->locallist != NULL))
		AddLineQueueX("pop %r", info->basereg);
#else
	AddLineQueueX("pop %r", basereg[ModuleInfo.Ofssize]);
#endif

	return;
}

/* ========================================================================================================= */
/* Win64 Calculate offsets of local variables and parameters from RBP    									 */
/*
----------------|
.				|
param 1			|
param 0			|
----------------|
return addr		|
----------------|
rbp				|
----------------|
gpr 0			|
gpr 1			|
.				|
----------------|---------
pad0?			| sub rsp,N
----------------|
xmm 0			|
xmm 1			|
.				|
----------------|
local 0			|
local 1			|
.				|
----------------|
shadow space    |
----------------|---------
				| mov rbp,rsp
----------------|
*/
/* ========================================================================================================= */
static void SetLocalOffsets_RBP(struct proc_info *info)
{
	struct dsym *curr     = NULL;
	int         cntxmm    = 0;
	int         cntstd    = 0;
	int         start     = 0;
	int         rspalign  = TRUE;
	int         align     = CurrWordSize;
	int         cnt       = 0;
	uint_16     *regs     = NULL;
	int         stackAdj  = 0;
	int         paramBase = 0;
	int         curOfs    = 0;
	int         resstack  = ((ModuleInfo.win64_flags & W64F_AUTOSTACKSP) ? sym_ReservedStack->value : 0);

	/* Check if the procedure requires 16byte alignment of all locals */
	if (ModuleInfo.win64_flags & W64F_STACKALIGN16)
		align = 16;

	/* Check if the procedure can have FPO */
	check_proc_fpo(info);

	/* Count USED registers (gpr, xmm, ymm, zmm) */
	if (info->regslist)
	{
		for (regs = info->regslist, cnt = *regs++; cnt; cnt--, regs++)
		{
			if (GetValueSp(*regs) & OP_XMM)
				cntxmm++;
			else if (GetValueSp(*regs) & OP_YMM)
				cntxmm += 2;
			else if (GetValueSp(*regs) & OP_ZMM)
				cntxmm += 4;
			else
				cntstd++;
		}
	}

	/* XMM registes are not pushed, so they require local space */
	info->localsize = (16 * cntxmm);

	/* Calculate total space required for locals */
	for (curr = info->locallist; curr; curr = curr->nextlocal) 
	{
		uint_32 totalsize = curr->sym.total_size;
		if (totalsize >= 16)
			totalsize = ROUND_UP(totalsize, 16);
		else if (totalsize >= 8 && totalsize < 16)
			totalsize = ROUND_UP(totalsize, 8);
		else if (totalsize >= 4 && totalsize < 8)
			totalsize = ROUND_UP(totalsize, 4);
		//uint_32 itemsize = (curr->sym.total_size == 0 ? 0 : curr->sym.total_size / curr->sym.total_length);
		//itemsize = ROUND_UP(itemsize, align);
		//if (curr->sym.total_size > align)
//			itemsize = ROUND_UP(curr->sym.total_size, align);
		//info->localsize += itemsize;
		info->localsize += totalsize;
	}
	info->localsize = ROUND_UP(info->localsize, 16);

	info->frameofs = 0;
	if (!info->fpo)
	{
		info->frameofs = (info->localsize >> 1) + resstack; /* Center the stack frame for optimised 1 byte displacements */
		info->frameofs = ROUND_UP(info->frameofs, 16);
		if (info->frameofs > 128) info->frameofs = 128;
	}

	/* adjust stack to be 16byte aligned if required */
	/* or at least account for odd pushed gprs */
	if (info->fpo)
	{
		if (info->pushed_reg % 2 == 0 && info->localsize % 16 == 0)
			stackAdj = 8;
		else if (info->pushed_reg % 2 == 0 && info->localsize % 16 != 0)
			stackAdj = 0;
		else if (info->pushed_reg % 2 != 0 && info->localsize % 16 == 0)
			stackAdj = 0;
		else if (info->pushed_reg % 2 != 0 && info->localsize % 16 != 0)
			stackAdj = 8;
	}
	else
	{
		if (info->pushed_reg % 2 == 0 && info->localsize % 16 == 0)
			stackAdj = 0;
		else if (info->pushed_reg % 2 == 0 && info->localsize % 16 != 0)
			stackAdj = 8;
		else if (info->pushed_reg % 2 != 0 && info->localsize % 16 == 0)
			stackAdj = 8;
		else if (info->pushed_reg % 2 != 0 && info->localsize % 16 != 0)
			stackAdj = 0;
	}

	/* Now set local offsets */
	curOfs = info->localsize + resstack - (16 * cntxmm) - info->frameofs;
	/*for (curr = info->locallist; curr; curr = curr->nextlocal)
	{
		int itemsize = (curr->sym.total_size == 0 ? 0 : curr->sym.total_size / curr->sym.total_length);
		itemsize = ROUND_UP(itemsize, align);
		if (curr->sym.total_size > align)
			itemsize = ROUND_UP(curr->sym.total_size, align);
		curr->sym.offset = curOfs - itemsize;
		curOfs -= itemsize;
	}*/

	for (curr = info->locallist; curr; curr = curr->nextlocal)
	{
		uint_32 totalsize = curr->sym.total_size;
		if (totalsize >= 16)
		{
			totalsize = ROUND_UP(totalsize, 16);
			curr->sym.offset = curOfs - totalsize;
			curOfs -= totalsize;
		}
	}
	for (curr = info->locallist; curr; curr = curr->nextlocal)
	{
		uint_32 totalsize = curr->sym.total_size;
		if (totalsize >= 8 && totalsize < 16)
		{
			totalsize = ROUND_UP(totalsize, 8);
			curr->sym.offset = curOfs - totalsize;
			curOfs -= totalsize;
		}
	}
	for (curr = info->locallist; curr; curr = curr->nextlocal)
	{
		uint_32 totalsize = curr->sym.total_size;
		if (totalsize >= 4 && totalsize < 8)
		{
			totalsize = ROUND_UP(totalsize, 4);
			curr->sym.offset = curOfs - totalsize;
			curOfs -= totalsize;
		}
	}
	for (curr = info->locallist; curr; curr = curr->nextlocal)
	{
		uint_32 totalsize = curr->sym.total_size;
		if (totalsize < 4)
		{
			curr->sym.offset = curOfs - totalsize;
			curOfs -= totalsize;
		}
	}

	/* Set parameter positions based on stack layout */
	if (info->fpo)
	{
		paramBase = (CurrWordSize * cntstd) + 8 + info->localsize + stackAdj + resstack - info->frameofs;
		for (curr = info->paralist; curr; curr = curr->nextparam)
			curr->sym.offset = paramBase + ((cnt++)*CurrWordSize);
	}
	else
	{
		paramBase = (CurrWordSize * cntstd) + 16 + info->localsize + stackAdj + resstack - info->frameofs;
		for (curr = info->paralist; curr; curr = curr->nextparam)
			curr->sym.offset = paramBase + ((cnt++)*CurrWordSize);
	}
}

/* ========================================================================================================= */
/* Win64 Calculate offsets of local variables and parameters from RSP    									 */
/* ========================================================================================================= */
static void SetLocalOffsets_RSP(struct proc_info *info)
{
	struct              dsym *curr;
	int                 cntxmm = 0;
	int                 cntstd = 0;
	int                 start = 0;
	uint_16             *regist;
	int                 cnt;
	unsigned char       xmmflag = 1;
	unsigned char       ymmflag = 0;
	unsigned			localadj;
	unsigned			paramadj;
	int                 rspalign = FALSE;
	int                 align = CurrWordSize;
	unsigned char       zmmflag = 0;
	regist = info->regslist;
	rspalign = TRUE;
	/* in 64-bit, if the FRAME attribute is set, the space for the registers
	* saved by the USES clause is located ABOVE the local variables!
	* v2.09: if stack space is to be reserved for INVOKE ( option WIN64:2 ),
	* the registers are also saved ABOVE the local variables.
	*/
	if (info->regslist) {
		for (cnt = *regist++; cnt; cnt--, regist++) {
			if (GetValueSp(*regist) & OP_XMM)
				xmmflag = 1;
			else if (GetValueSp(*regist) & OP_YMM)
				ymmflag = 1;
			else if (GetValueSp(*regist) & OP_ZMM)
				zmmflag = 1;
		}
	}
	if (ymmflag) XYZMMsize = 32;
	else XYZMMsize = 16;

	if (info->fpo || rspalign) {
		/* count registers to be saved ABOVE local variables.
		* v2.06: the list may contain xmm registers, which have size 16!
		*/
		if (info->regslist) {
			int         cnt;
			uint_16     *regs;
			for (regs = info->regslist, cnt = *regs++; cnt; cnt--, regs++)
				if ((GetValueSp(*regs) & OP_XMM) || (GetValueSp(*regs) & OP_YMM) || (GetValueSp(*regs) & OP_ZMM))
					cntxmm++;
				else
					cntstd++;
		}
		/* in case there's no frame register, adjust start offset. */
		if (info->parasize == 0 && info->locallist == NULL)
			start = CurrWordSize;
		cntstd = info->pushed_reg;
		if (rspalign && cntxmm) {
			if (!(cntstd & 1)) info->localsize += 8;
			info->localsize += XYZMMsize * cntxmm;
		}
		DebugMsg1(("SetLocalOffsets_RSP(%s): cntxmm=%u cntstd=%u start=%u align=%u localsize=%u\n", CurrProc->sym.name, cntxmm, cntstd, start, align, info->localsize));
	}
	/* scan the locals list and set member sym.offset */
	for (curr = info->locallist; curr; curr = curr->nextlocal)
	{
		uint_32 itemsize = (curr->sym.total_size == 0 ? 0 : curr->sym.total_size / curr->sym.total_length);

		int n = 0;
		if (curr->sym.isarray) n = curr->sym.total_size & 0x7;

		if (itemsize < 16)
			info->localsize = ROUND_UP(info->localsize, itemsize);

		if (ModuleInfo.win64_flags & W64F_STACKALIGN16 && curr->sym.total_size > CurrWordSize)
			info->localsize = ROUND_UP(info->localsize, 16);

		curr->sym.offset = info->localsize;
		info->localsize += curr->sym.total_size + n;
		if (itemsize > align)
			info->localsize = ROUND_UP(info->localsize, align);
		else if (itemsize) /* v2.04: skip if size == 0 */
			info->localsize = ROUND_UP(info->localsize, itemsize);

		DebugMsg1(("SetLocalOffsets_RSP(%s): offset of %s (size=%u) set to %d\n", CurrProc->sym.name, curr->sym.name, curr->sym.total_size, curr->sym.offset));
	}

	if (!(cntstd & 1) && ((info->localsize & 15) == 0)) info->localsize += 8;

	/* v2.11: localsize must be rounded before offset adjustment if fpo */
	/* RSP 16-byte alignment? */
	if (rspalign)
		info->localsize = ROUND_UP(info->localsize, 8);
	DebugMsg1(("SetLocalOffsets_RSP(%s): localsize=%u after processing locals\n", CurrProc->sym.name, info->localsize));

	/* v2.11: recalculate offsets for params and locals if there's no frame pointer.
	* Problem in 64-bit: option win64:2 triggers the "stack space reservation" feature -
	* but the final value of this space is known at the procedure's END only.
	* Hence in this case the values calculated below are "preliminary".
	*/
	if (info->fpo) {

		if (rspalign) {
			localadj = info->localsize;
			paramadj = info->localsize - CurrWordSize - start;
		}
		else
		{
			localadj = info->localsize + cntstd * CurrWordSize;
			paramadj = info->localsize + cntstd * CurrWordSize - CurrWordSize;
		}
	}
}

#endif

#if SYSV_SUPPORT

/* ========================================================================================================= */
/* the SYSTEMV 64 ABI is strict: the six parameters are passed in registers. */
/* ========================================================================================================= */
static int sysv_pcheck(struct dsym *proc, struct dsym *paranode, int *used, int *vecused)
/***************************************************************************/
{
	char regname[32];
	int size = SizeFromMemtype(paranode->sym.mem_type, paranode->sym.Ofssize, paranode->sym.type);

	paranode->sym.string_ptr = NULL; // Ensure it's null first.

	//===============================================================================================================
	// Handle Vector -> SIMD Parameter Types
	//===============================================================================================================
	// Parameter is either XMM, float, double or __M128
	if ((paranode->sym.mem_type == MT_REAL4) || (paranode->sym.mem_type == MT_REAL8) || (paranode->sym.mem_type == MT_TYPE && _stricmp(paranode->sym.type->name, "__m128") == 0) || paranode->sym.mem_type == MT_OWORD)
	{
		if (*vecused >= 8)
		{
			paranode->sym.string_ptr = NULL;
			return(0);
		}
		paranode->sym.state = SYM_TMACRO;
		GetResWName(sysV64_regsXMM[*vecused], regname);
		paranode->sym.tokval = sysV64_regsXMM[*vecused]; /* Store register tokval so invoke can use it */
		paranode->sym.total_size = 0;
		paranode->sym.string_ptr = LclAlloc(strlen(regname) + 1);
		strcpy(paranode->sym.string_ptr, regname);
		(*vecused)++;
		proc->e.procinfo->firstVEC = *vecused;
		return(1);
	}
	// Parameter is either YMM or __m256
	if ((paranode->sym.mem_type == MT_TYPE && _stricmp(paranode->sym.type->name, "__m256") == 0) || paranode->sym.mem_type == MT_YMMWORD)
	{
		if (*vecused >= 8)
		{
			paranode->sym.string_ptr = NULL;
			return(0);
		}
		paranode->sym.state = SYM_TMACRO;
		GetResWName(sysV64_regsYMM[*vecused], regname);
		paranode->sym.tokval = sysV64_regsYMM[*vecused]; /* Store register tokval so invoke can use it */
		paranode->sym.total_size = 0;
		paranode->sym.string_ptr = LclAlloc(strlen(regname) + 1);
		strcpy(paranode->sym.string_ptr, regname);
		(*vecused)++;
		proc->e.procinfo->firstVEC = *vecused;
		return(1);
	}
	// Parameter is either ZMM or __m512
	if ((paranode->sym.mem_type == MT_TYPE && _stricmp(paranode->sym.type->name, "__m512") == 0) || paranode->sym.mem_type == MT_ZMMWORD)
	{
		if (*vecused >= 8)
		{
			paranode->sym.string_ptr = NULL;
			return(0);
		}
		paranode->sym.state = SYM_TMACRO;
		GetResWName(sysV64_regsZMM[*vecused], regname);
		paranode->sym.tokval = sysV64_regsZMM[*vecused]; /* Store register tokval so invoke can use it */
		paranode->sym.total_size = 0;
		paranode->sym.string_ptr = LclAlloc(strlen(regname) + 1);
		strcpy(paranode->sym.string_ptr, regname);
		(*vecused)++;
		proc->e.procinfo->firstVEC = *vecused;
		return(1);
	}
	if (paranode->sym.mem_type == MT_TYPE)
	{
		/* Unsupported argument type */
		EmitErr(INVOKE_ARGUMENT_NOT_SUPPORTED);
		return(0);
	}

	//===============================================================================================================
	// HANDLE Integer -> GPR Parameter Types
	//===============================================================================================================
	if (size > CurrWordSize || *used >= 6 || paranode->sym.is_vararg)
	{
		paranode->sym.string_ptr = NULL;
		return(0);
	}
	paranode->sym.state = SYM_TMACRO;

	/* v2.29: for codeview debug info, store the register index in the symbol */
	switch (size)
	{
	case 8:
		GetResWName(sysV64_regs[*used], regname);
		paranode->sym.total_size = 8;
		paranode->sym.tokval = sysV64_regs[*used];   /* Store register tokval so invoke can use it */
		break;
	case 4:
		GetResWName(sysV64_regs32[*used], regname);
		paranode->sym.total_size = 4;
		paranode->sym.tokval = sysV64_regs32[*used]; /* Store register tokval so invoke can use it */
		break;
	case 2:
		GetResWName(sysV64_regs16[*used], regname);
		paranode->sym.total_size = 2;
		paranode->sym.tokval = sysV64_regs16[*used]; /* Store register tokval so invoke can use it */
		break;
	case 1:
		GetResWName(sysV64_regs8[*used], regname);
		paranode->sym.total_size = 1;
		paranode->sym.tokval = sysV64_regs8[*used];  /* Store register tokval so invoke can use it */
		break;
	}

	paranode->sym.string_ptr = LclAlloc(strlen(regname) + 1);
	strcpy(paranode->sym.string_ptr, regname);
	(*used)++;
	proc->e.procinfo->firstGPR = *used;
	return(1);
}

static void sysv_return(struct dsym *proc, char *buffer)
/********************************************************/
{
	return;
}

/* ========================================================================================================= */
/* sysv default prologue when PROC FRAME and OPTION FRAME:AUTO is set */
/* ========================================================================================================= */
static void write_sysv_default_prologue_RBP(struct proc_info *info)
/****************************************************************/
{
	uint_16             *regist;
	int                 i = 0;
	int                 cnt;
	int                 cntxmm;
	int                 stackadj = 0;
	int                 resstack = ((ModuleInfo.win64_flags & W64F_AUTOSTACKSP) ? sym_ReservedStack->value : 0);

	info->pushed_reg = 0;

	//if (info->stackAdj % 16 != 0) stackadj = 8;

	/* Only setup a stack-frame for RBP if there are locals or parameters */
	stackadj += 8;
	if (!info->fpo && GetRegNo(info->basereg) != 4 && (info->parasize != 0 || info->locallist != NULL))
	{
		AddLineQueueX("push %r", info->basereg);
		AddLineQueueX("mov %r, %r", info->basereg, T_RSP);
		stackadj -= 8;
	}
	/* after the "push rbp", the stack is xmmword aligned (except if we didn't push rbp) */

	/* Push the USED GPR registers */
	cntxmm = 0;
	if (info->regslist)
	{
		regist = info->regslist;
		for (cnt = *regist++; cnt; cnt--, regist++)
		{
			/* AVX registers will be multiplied with their correct size; 2.26 */
			if (GetValueSp(*regist) & OP_XMM)
				cntxmm += 1;                         // 1 * 16
			else if (GetValueSp(*regist) & OP_YMM)
				cntxmm += 2;                         // 2 * 16		
			else if (GetValueSp(*regist) & OP_ZMM)
				cntxmm += 4;                         // 4 * 16
			else
			{
				info->pushed_reg += 1;
				AddLineQueueX("push %r", *regist);
			}
		}
	}

	/* Ensure RSP is aligned 16 */
	/*	gprOdd = (info->pushed_reg & 1);
	if (stackadj == 0 && gprOdd) stackadj += 8;
	else if (stackadj == 8 && !gprOdd && info->pushed_reg>0) stackadj -= 8;
	if (info->localsize == 8 && stackadj == 8)
	stackadj = 0;
	*/

	if (info->fpo)
	{
		if (info->pushed_reg % 2 == 0 && info->pushed_reg > 0)
			stackadj += 8;
		else if (info->pushed_reg % 2 == 0)
			stackadj += 0;
	}
	else
	{
		if (info->pushed_reg % 2 == 0)
			stackadj += 0;
		else
			stackadj += 8;
	}

	/* Allocate space for local variables */
	if ((info->localsize + resstack) > 0)
	{
		DebugMsg1(("write_sysv_default_prologue_RBP: localsize=%u\n", info->localsize));
		/* SUB  RSP, localsize */
		if (ModuleInfo.redzone == 1 && (info->localsize + resstack) < 128 && resstack == 0)
			;
		else
		{
			// localsize includes the saved xmms, restack valid and a multiple of 16 or 0.
			if (Options.frameflags)
			{
				AddLineQueueX("lea %r, [%r-%d]", T_RSP, T_RSP, NUMQUAL(info->localsize + stackadj + resstack));
			}
			else
			{
				AddLineQueueX("sub %r, %d", T_RSP, NUMQUAL(info->localsize + stackadj + resstack));
			}
		}
	}
	/* No locals, still account for stackadj but only if not a leaf */
	else if (stackadj > 0 && !info->isleaf)
	{
		if (Options.frameflags)
		{
			AddLineQueueX("lea %r, [%r-%d]", T_RSP, T_RSP, NUMQUAL(stackadj + resstack));
		}
		else
		{
			AddLineQueueX("sub %r, %d", T_RSP, NUMQUAL(stackadj + resstack));
		}
		info->stackAdj = stackadj;
	}

	/* save USED vector registers */
	if (cntxmm)
	{
		regist = info->regslist;
		i = (info->localsize + resstack - cntxmm * 16) & ~(16 - 1);
		if (regist)
		{
			for (cnt = *regist++; cnt; cnt--, regist++)
			{
				if (GetValueSp(*regist) & OP_XMM) {
					AddLineQueueX("%s [%r+%u], %r", MOVE_ALIGNED_INT(), T_RSP, NUMQUAL i, *regist);
					i += 16;
				}
				else if (GetValueSp(*regist) & OP_YMM) {
					AddLineQueueX("%s [%r+%u], %r", MOVE_UNALIGNED_INT(), T_RSP, NUMQUAL i, *regist);
					i += 32;
				}
				else if (GetValueSp(*regist) & OP_ZMM) {
					AddLineQueueX("%s [%r+%u+%s], %r", MOVE_UNALIGNED_INT(), T_RSP, NUMQUAL i, *regist);
					i += 64;
				}
			}
		}
	}
	return;
}

/* ========================================================================================================= */
/* SYSTEM V default epilogue if PROC FRAME and OPTION FRAME:AUTO is set for RBP stackbase */
/* ========================================================================================================= */
static void write_sysv_default_epilogue_RBP(struct proc_info *info)
/****************************************************************/
{
	int  resstack = ((ModuleInfo.win64_flags & W64F_AUTOSTACKSP) ? sym_ReservedStack->value : 0);
	int  stackadj = 8;

	if (!info->fpo && GetRegNo(info->basereg) != 4 && (info->parasize != 0 || info->locallist != NULL))
	{
		stackadj -= 8;
	}

	if (info->fpo)
	{
		if (info->pushed_reg % 2 == 0 && info->pushed_reg != 0)
			stackadj += 8;
		else if (info->pushed_reg != 0)
			stackadj += 0;
	}
	else
	{
		if (info->pushed_reg % 2 == 0 && info->pushed_reg != 0)
			stackadj += 0;
		else if (info->pushed_reg != 0)
			stackadj += 8;
	}

	/* Restore USED vector registers */
	if (info->regslist)
	{
		uint_16 *regs;
		int cnt;
		int i;

		for (regs = info->regslist, cnt = *regs++, i = 0; cnt; cnt--, regs++)
			if (GetValueSp(*regs) & OP_XMM)
				i++;
			else if (GetValueSp(*regs) & OP_YMM)
				i += 2;
			else if (GetValueSp(*regs) & OP_ZMM)
				i += 4;

		DebugMsg1(("write_sysv_default_epilogue(%s): %u xmm registers to restore\n", CurrProc->sym.name, i));

		if (i)
		{
			i = (info->localsize - i * 16) & ~(16 - 1);
			for (regs = info->regslist, cnt = *regs++; cnt; cnt--, regs++)
			{
				if (GetValueSp(*regs) & OP_XMM)
				{
					AddLineQueueX("%s %r, [%r + %u]", MOVE_ALIGNED_INT(), *regs, stackreg[ModuleInfo.Ofssize], NUMQUAL i);
					i += 16;
				}
				if (GetValueSp(*regs) & OP_YMM)
				{
					AddLineQueueX("%s %r, [%r + %u]", MOVE_UNALIGNED_INT(), *regs, stackreg[ModuleInfo.Ofssize], NUMQUAL i);
					i += 32;
				}
				if (GetValueSp(*regs) & OP_ZMM)
				{
					AddLineQueueX("%s %r, [%r + %u]", MOVE_UNALIGNED_INT(), *regs, stackreg[ModuleInfo.Ofssize], NUMQUAL i);
					i += 64;
				}
			}
		}
	}

	/* No Sub RSP, use RedZone optimisation */
	if (ModuleInfo.redzone == 1 && (info->localsize + resstack < 128) && resstack == 0)
		;
	else if (info->localsize > 0)
	{
		if (Options.frameflags)
		{
			AddLineQueueX("lea %r, [%r+%d]", stackreg[ModuleInfo.Ofssize], stackreg[ModuleInfo.Ofssize], NUMQUAL info->localsize + stackadj);
		}
		else
		{
			AddLineQueueX("add %r, %d", stackreg[ModuleInfo.Ofssize], NUMQUAL info->localsize + stackadj);
		}
	}
	else if (stackadj > 0 && !info->isleaf)
	{
		if (Options.frameflags)
		{
			AddLineQueueX("lea %r, [%r+%d]", stackreg[ModuleInfo.Ofssize], stackreg[ModuleInfo.Ofssize], NUMQUAL info->localsize + stackadj);
		}
		else
		{
			AddLineQueueX("add %r, %d", stackreg[ModuleInfo.Ofssize], NUMQUAL info->localsize + stackadj);
		}
	}

	pop_register(CurrProc->e.procinfo->regslist);

#if STACKBASESUPP
	if (!info->fpo && GetRegNo(info->basereg) != 4 && (info->parasize != 0 || info->locallist != NULL))
		AddLineQueueX("pop %r", info->basereg);
#else
	AddLineQueueX("pop %r", basereg[ModuleInfo.Ofssize]);
#endif
	return;
}

/* ========================================================================================================= */
/* SYSTEM V default stack frame offsets for RBP based frame */
/* ========================================================================================================= */
static void SetLocalOffsets_RBP_SYSV(struct proc_info *info)
{
	struct dsym *curr;
	int         cntxmm = 0;
	int         cntstd = 0;
	int         start = 0;
	int         rspalign = TRUE;
	int         align = CurrWordSize;
	align = 16;

	check_proc_fpo(info);

#if AMD64_SUPPORT || STACKBASESUPP
	/* in 64-bit, if the FRAME attribute is set, the space for the registers
	* saved by the USES clause is located ABOVE the local variables!
	* v2.09: if stack space is to be reserved for INVOKE ( option WIN64:2 ),
	* the registers are also saved ABOVE the local variables.
	*/
	if (info->fpo || rspalign) {
		/* count registers to be saved ABOVE local variables.
		* v2.06: the list may contain xmm registers, which have size 16!
		*/
		if (info->regslist) {
			int         cnt;
			uint_16     *regs;
			for (regs = info->regslist, cnt = *regs++; cnt; cnt--, regs++)
				if (GetValueSp(*regs) & OP_XMM)
					cntxmm++;
				else if (GetValueSp(*regs) & OP_YMM)
					cntxmm += 2;
				else if (GetValueSp(*regs) & OP_ZMM)
					cntxmm += 4;
				else
					cntstd++;
		}
		/* in case there's no frame register, adjust start offset. */
		if ((info->fpo || (info->parasize == 0 && info->locallist == NULL)))
			start = 0;
#if AMD64_SUPPORT
		if (rspalign)
		{
			info->localsize = start + (cntstd * CurrWordSize);

			if (cntxmm)
			{
				info->localsize += 16 * cntxmm;
				//info->localsize = ROUND_UP(info->localsize, 16);
			}
		}
#endif
		DebugMsg1(("SetLocalOffsets_RBP(%s): cntxmm=%u cntstd=%u start=%u align=%u localsize=%u\n", CurrProc->sym.name, cntxmm, cntstd, start, align, info->localsize));
	}
#endif

	/* scan the locals list and set member sym.offset */
	for (curr = info->locallist; curr; curr = curr->nextlocal) {
		uint_32 itemsize = (curr->sym.total_size == 0 ? 0 : curr->sym.total_size / curr->sym.total_length);
		info->localsize += curr->sym.total_size;
		if (itemsize > align) {
			if (itemsize == 32)
				info->localsize = ROUND_UP(info->localsize, 32);
			else if (itemsize == 16)
				info->localsize = ROUND_UP(info->localsize, 16);
			else
				info->localsize = ROUND_UP(info->localsize, align);
		}
		else if (itemsize) /* v2.04: skip if size == 0 */
			info->localsize = ROUND_UP(info->localsize, itemsize);
		curr->sym.offset = -info->localsize;//(cntstd*CurrWordSize) + (info->localsize));
		DebugMsg1(("SetLocalOffsets_RBP(%s): offset of %s (size=%u) set to %d\n", CurrProc->sym.name, curr->sym.name, curr->sym.total_size, curr->sym.offset));
	}

	/* v2.11: localsize must be rounded before offset adjustment if fpo */
	info->localsize = ROUND_UP(info->localsize, CurrWordSize);

	DebugMsg1(("SetLocalOffsets_RBP(%s): localsize=%u after processing locals\n", CurrProc->sym.name, info->localsize));

#if STACKBASESUPP
	/* v2.11: recalculate offsets for params and locals if there's no frame pointer.
	* Problem in 64-bit: option win64:2 triggers the "stack space reservation" feature -
	* but the final value of this space is known at the procedure's END only.
	* Hence in this case the values calculated below are "preliminary".
	*/
	if (info->fpo) {
		unsigned localadj;
		unsigned paramadj;
#if AMD64_SUPPORT
		if (rspalign) {
			localadj = (info->localsize + 8);
			paramadj = (info->localsize + 8) - CurrWordSize - start;
		}
		else {
#endif
			localadj = (info->localsize + 8) + cntstd * CurrWordSize;
			paramadj = (info->localsize + 8) + cntstd * CurrWordSize - CurrWordSize;
#if AMD64_SUPPORT
		}
#endif
		DebugMsg1(("SetLocalOffsets_RBP(%s): FPO, adjusting offsets\n", CurrProc->sym.name));
		/* subtract CurrWordSize value for params, since no space is required to save the frame pointer value */
		for (curr = info->locallist; curr; curr = curr->nextlocal) {
			DebugMsg1(("SetLocalOffsets_RBP(%s): FPO, offset for %s %4d -> %4d\n", CurrProc->sym.name, curr->sym.name, curr->sym.offset, curr->sym.offset + localadj));
			curr->sym.offset += localadj;
		}
		for (curr = info->paralist; curr; curr = curr->nextparam) {
			DebugMsg1(("SetLocalOffsets_RBP(%s): FPO, offset for %s %4d -> %4d\n", CurrProc->sym.name, curr->sym.name, curr->sym.offset, curr->sym.offset + paramadj));
			curr->sym.offset += paramadj;
		}
	}
#endif

#if AMD64_SUPPORT
	/* v2.12: if the space used for register saves has been added to localsize,
	* the part that covers "pushed" GPRs has to be subtracted now, before prologue code is generated.
	*/
	if (rspalign) {
		info->localsize -= cntstd * 8;
		info->localsize = ROUND_UP(info->localsize, align);
		//		if (info->isframe && ModuleInfo.frame_auto && info->localsize < 32 && info->localsize % 16 != 0)
		//		info->localsize = ROUND_UP(info->localsize, 16);
		DebugMsg1(("SetLocalOffsets_RBP(%s): final localsize=%u\n", CurrProc->sym.name, info->localsize));
	}
#endif
}

#endif


/* write PROC prologue
* this is to be done after the LOCAL directives
* and *before* any real instruction
*/
/* prolog code timings
best result
size  86  286  386  486  P     86  286  386  486  P
push bp       2     11  3    2    1    1
mov bp,sp     2     2   2    2    1    1
sub sp,immed  4     4   3    2    1    1
-----------------------------
8     17  8    6    3    3     x   x    x    x    x
push ebp      2     -   -    2    1    1
mov ebp,esp   2     -   -    2    1    1
sub esp,immed 6     -   -    2    1    1
-----------------------------
10    -   -    6    3    3              x    x    x
enter imm,0   4     -   11   10   14   11
write prolog code
*/

/* Write out generic prologue for 386, esp, watc, borland */
static ret_code write_generic_prologue(struct proc_info *info)
/********************************************/
{
	uint_16             *regist;
	int                 cnt;
	int                 resstack = 0;
	int					stackadj = 0;

	regist = info->regslist;
	check_proc_fpo(info);

	if (info->fpo)
	{
		if (info->pushed_reg % 2 == 0 && info->localsize % 16 == 0)
			stackadj = 8;
		else if (info->pushed_reg % 2 == 0 && info->localsize % 16 != 0)
			stackadj = 0;
		else if (info->pushed_reg % 2 != 0 && info->localsize % 16 == 0)
			stackadj = 0;
		else if (info->pushed_reg % 2 != 0 && info->localsize % 16 != 0)
			stackadj = 8;
	}
	else
	{
		if (info->pushed_reg % 2 == 0 && info->localsize % 16 == 0)
			stackadj = 0;
		else if (info->pushed_reg % 2 == 0 && info->localsize % 16 != 0)
			stackadj = 8;
		else if (info->pushed_reg % 2 != 0 && info->localsize % 16 == 0)
			stackadj = 8;
		else if (info->pushed_reg % 2 != 0 && info->localsize % 16 != 0)
			stackadj = 0;
	}

	/* default processing. if no params/locals are defined, continue */
	if (info->forceframe == FALSE && info->localsize == 0 &&
		info->stackparam == FALSE && info->has_vararg == FALSE &&
		resstack == 0 && info->regslist == NULL && !info->fpo)
		return(NOT_ERROR);

	if (info->fpo && stackadj > 0 && CurrProc->sym.langtype == LANG_FASTCALL && !info->isleaf)
	{
		if (Options.frameflags)
		{
			AddLineQueueX("lea %r, [%r-%d]", T_RSP, T_RSP, stackadj);
		}
		else
		{
			AddLineQueueX("sub %r, %d", T_RSP, stackadj);
		}
	}

	/* initialize shadow space for register params */
	if (ModuleInfo.Ofssize == USE64 && ModuleInfo.fctype == FCT_WIN64 && (ModuleInfo.win64_flags & W64F_SAVEREGPARAMS))
	{
		if (CurrProc->sym.langtype == LANG_FASTCALL && ModuleInfo.basereg[ModuleInfo.Ofssize] == T_RSP)
			win64_SaveRegParams_RSP(info);
		else if (CurrProc->sym.langtype == LANG_FASTCALL && ModuleInfo.basereg[ModuleInfo.Ofssize] == T_RBP)
			win64_SaveRegParams_RBP(info);
	}

	if (info->locallist || info->stackparam || info->has_vararg || info->forceframe)
	{
		/* write 80386 prolog code
		* PUSH [E|R]BP
		* MOV  [E|R]BP, [E|R]SP
		* SUB  [E|R]SP, localsize
		*/
		if (!info->fpo) {
			AddLineQueueX("push %r", info->basereg);
			AddLineQueueX("mov %r, %r", info->basereg, stackreg[ModuleInfo.Ofssize]);
		}
	}
	if (resstack)
	{
		/* in this case, push the USES registers BEFORE the stack space is reserved */
		if (regist) {
			for (cnt = *regist++; cnt; cnt--, regist++)
				AddLineQueueX("push %r", *regist);
			regist = NULL;
		}
		if (Options.frameflags)
		{
			AddLineQueueX("lea %r, [%r-(%d+%s)]", stackreg[ModuleInfo.Ofssize], stackreg[ModuleInfo.Ofssize], NUMQUAL info->localsize, sym_ReservedStack->name);
		}
		else
		{
			AddLineQueueX("sub %r, %d + %s", stackreg[ModuleInfo.Ofssize], NUMQUAL info->localsize, sym_ReservedStack->name);
		}
	}
	else
	{
		if (info->localsize)
		{
			if (Options.frameflags)
			{
				AddLineQueueX("lea %r, [%r-%d]", stackreg[ModuleInfo.Ofssize], stackreg[ModuleInfo.Ofssize], info->localsize);
			}
			else
			{
				/* using ADD and the 2-complement has one advantage:
				* it will generate short instructions up to a size of 128.
				* with SUB, short instructions work up to 127 only.
				*/
				if (Options.masm_compat_gencode || info->localsize <= 128)
					AddLineQueueX("add %r, %d", stackreg[ModuleInfo.Ofssize], NUMQUAL - info->localsize);
				else
					AddLineQueueX("sub %r, %d", stackreg[ModuleInfo.Ofssize], NUMQUAL info->localsize);
			}
		}
	}

	if (info->loadds) {
		AddLineQueueX("push %r", T_DS);
		AddLineQueueX("mov %r, %s", T_AX, szDgroup);
		AddLineQueueX("mov %r, %r", T_DS, ModuleInfo.Ofssize ? T_EAX : T_AX);
	}

	/* Push the GPR registers of the USES clause */
	if (regist) {
		for (cnt = *regist++; cnt; cnt--, regist++) {
			AddLineQueueX("push %r", *regist);
		}
	}
}

/* Write out UASM internal prologue */
static ret_code write_default_prologue(void)
/********************************************/
{
	struct proc_info    *info;
	uint_8              oldlinenumbers;
	int                 resstack = 0;
	bool                OldState = FALSE;

	info = CurrProc->e.procinfo;

	if (ModuleInfo.Ofssize == USE64 && ModuleInfo.fctype == FCT_WIN64 && (ModuleInfo.win64_flags & W64F_AUTOSTACKSP))
		resstack = sym_ReservedStack->value;

	if (ModuleInfo.Ofssize == USE64)
	{
		if (ModuleInfo.basereg[USE64] == T_RSP)
			write_win64_default_prologue_RSP(info);
		else if ((ModuleInfo.basereg[USE64] == T_RBP) && CurrProc->sym.langtype == LANG_FASTCALL && info->isframe)
			write_win64_default_prologue_RBP(info);
		else if ((ModuleInfo.basereg[USE64] == T_RBP) && CurrProc->sym.langtype == LANG_FASTCALL)
			write_generic_prologue(info);
		else if ((ModuleInfo.basereg[USE64] == T_RBP) && CurrProc->sym.langtype == LANG_SYSVCALL)
			write_sysv_default_prologue_RBP(info);

		/* v2.11: line queue is now run here */
		goto runqueue;
		return(NOT_ERROR);
	}
	else
	{
		write_generic_prologue(info);
	}

runqueue:

	/* special case: generated code runs BEFORE the line.*/
	if (ModuleInfo.list && UseSavedState)
		if (Parse_Pass == PASS_1)
			info->prolog_list_pos = list_pos;
		else
			list_pos = info->prolog_list_pos;

	/* line number debug info also needs special treatment
	* because current line number is the first true src line
	* IN the proc.
	*/
	oldlinenumbers = Options.line_numbers;
	Options.line_numbers = FALSE; /* temporarily disable line numbers */
	OldState = UseSavedState; /* UASM 2.56 - we need this to ensure we don't accidental generate duplicate symbol definitions */
	UseSavedState = FALSE;
	RunLineQueue();
	UseSavedState = OldState;
	Options.line_numbers = oldlinenumbers;

	if (ModuleInfo.list && UseSavedState && (Parse_Pass > PASS_1))
		LineStoreCurr->list_pos = list_pos;

	return(NOT_ERROR);
}

/* Set Local offsets for 32bit procedures */
static void SetLocalOffsets(struct proc_info *info)
/***************************************************/
{
	struct dsym *curr;
	int		cntxmm = 0;
	int		cntstd = 0;
	int		start = 0;
	int		rspalign = FALSE;
	int		align = CurrWordSize;

	if (info->isframe || (ModuleInfo.fctype == FCT_WIN64 && (ModuleInfo.win64_flags & W64F_AUTOSTACKSP))) {
		rspalign = TRUE;
		if (ModuleInfo.win64_flags & W64F_STACKALIGN16)
			align = 16;
	}
	/* in 64-bit, if the FRAME attribute is set, the space for the registers
	* saved by the USES clause is located ABOVE the local variables!
	* v2.09: if stack space is to be reserved for INVOKE ( option WIN64:2 ),
	* the registers are also saved ABOVE the local variables.
	*/
	if (info->fpo || rspalign) {
		/* count registers to be saved ABOVE local variables.
		* v2.06: the list may contain xmm registers, which have size 16!
		*/
		if (info->regslist) {
			int		cnt;
			uint_16	*regs;
			for (regs = info->regslist, cnt = *regs++; cnt; cnt--, regs++)
				if (GetValueSp(*regs) & OP_XMM)
					cntxmm++;
				else
					cntstd++;
		}
		/* in case there's no frame register, adjust start offset. */
		if ((info->fpo || (info->parasize == 0 && info->locallist == NULL)))
			start = CurrWordSize;
		if (rspalign) {
			info->localsize = start + cntstd * CurrWordSize;
			if (cntxmm) {
				info->localsize += 16 * cntxmm;
				info->localsize = ROUND_UP(info->localsize, 16);
			}
		}
	}

	/* scan the locals list and set member sym.offset */
	for (curr = info->locallist; curr; curr = curr->nextlocal) {
		uint_32 itemsize = (curr->sym.total_size == 0 ? 0 : curr->sym.total_size / curr->sym.total_length);
		info->localsize += curr->sym.total_size;
		if (itemsize > align)
			info->localsize = ROUND_UP(info->localsize, align);
		else if (itemsize) { /* v2.04: skip if size == 0 */
			if ((CurrWordSize == 4) && (itemsize == 3)) itemsize = CurrWordSize; /* fix v2.49 (32bit only) */
			info->localsize = ROUND_UP(info->localsize, itemsize);
		}
		curr->sym.offset = -info->localsize;
	}

	/* v2.11: localsize must be rounded before offset adjustment if fpo */
	info->localsize = ROUND_UP(info->localsize, CurrWordSize);
	/* RSP 16-byte alignment? */
	if (rspalign) {
		info->localsize = ROUND_UP(info->localsize, 16);
	}

	/* v2.11: recalculate offsets for params and locals if there's no frame pointer.
	* Problem in 64-bit: option win64:2 triggers the "stack space reservation" feature -
	* but the final value of this space is known at the procedure's END only.
	* Hence in this case the values calculated below are "preliminary".
	*/
	if (info->fpo) {
		unsigned localadj;
		unsigned paramadj;
		if (rspalign) {
			localadj = info->localsize;
			paramadj = info->localsize - CurrWordSize - start;
		}
		else {
			localadj = info->localsize + cntstd * CurrWordSize;
			paramadj = info->localsize + cntstd * CurrWordSize - CurrWordSize;
		}

		/* subtract CurrWordSize value for params, since no space is required to save the frame pointer value */
		for (curr = info->locallist; curr; curr = curr->nextlocal) {
			curr->sym.offset += localadj;
		}

		if (info->stored_reg != 1) // UASM 2.42 only adjust parameters once.
		{
			info->stored_reg = 1;
			for (curr = info->paralist; curr; curr = curr->nextparam) {
				curr->sym.offset += paramadj;
			}
		}
	}

	/* v2.12: if the space used for register saves has been added to localsize,
	* the part that covers "pushed" GPRs has to be subtracted now, before prologue code is generated.
	*/
	if (rspalign) {
		info->localsize -= cntstd * 8 + start;
	}
}

void write_prologue(struct asm_tok tokenarray[])
/************************************************/
{
	struct dsym *curr;
	int		align = CurrWordSize;

	/* reset @ProcStatus flag */
	ProcStatus &= ~PRST_PROLOGUE_NOT_DONE;
	CurrProc->e.procinfo->prologueDone = FALSE;

	if (Parse_Pass == PASS_1)
		CurrProc->e.procinfo->fpo = FALSE;
	if (ModuleInfo.basereg[USE64] == T_RSP)
		CurrProc->e.procinfo->fpo = TRUE;

	if (ModuleInfo.fctype == FCT_WIN64 && (ModuleInfo.win64_flags & W64F_AUTOSTACKSP))
	{
		/* in pass one init reserved stack with 4*8 to force stack frame creation */
		sym_ReservedStack->value = (Parse_Pass == PASS_1 ? 4 * sizeof(uint_64) : CurrProc->e.procinfo->ReservedStack);
		if (Parse_Pass == PASS_1)
		{
			sym_ReservedStack->value = 0;
		}
	}

	/* UASM 2.42 - Any proc with no prologue will have no stack frame, so set fpo and force use of esp if option stackbase:xSP is set. */
	if (ModuleInfo.prologuemode == PEM_NONE && CurrProc->e.procinfo->forceframe == FALSE && (CurrProc->e.procinfo->basereg == T_ESP))
	{
		CurrProc->e.procinfo->fpo = TRUE;
		if (CurrProc->e.procinfo->localsize > 0)
			AddLineQueueX("sub esp,%d", CurrProc->e.procinfo->localsize);
		RunLineQueue();
	}

	if (ModuleInfo.Ofssize == USE64)
	{
		if (ModuleInfo.basereg[USE64] == T_RSP)
		{
			if (Parse_Pass == PASS_1)
				SetLocalOffsets_RSP(CurrProc->e.procinfo);
		}
		else
		{
			/* We need this to run over multiple passes to ensure FPO is handled */
			CurrProc->e.procinfo->localsize = 0;
			if ((Options.output_format == OFORMAT_COFF || Options.output_format == OFORMAT_BIN) && CurrProc->e.procinfo->isframe)
				SetLocalOffsets_RBP(CurrProc->e.procinfo); 
			else if ((Options.output_format == OFORMAT_ELF || Options.output_format == OFORMAT_MAC) && Options.sub_format == SFORMAT_64BIT)
				SetLocalOffsets_RBP_SYSV(CurrProc->e.procinfo);
			else
				SetLocalOffsets(CurrProc->e.procinfo);
		}
	}
	else
	{
		//if (Parse_Pass == PASS_1)  /* UASM 2.42 allow 32bit version to run across multiple passes to support FPO */
		if (Parse_Pass > PASS_1)
			CurrProc->e.procinfo->localsize = 0; // reset per pass.
		SetLocalOffsets(CurrProc->e.procinfo);
	}

	ProcStatus |= PRST_INSIDE_PROLOGUE;

	/* there are 3 cases:
	* option prologue:NONE           proc_prologue == NULL
	* option prologue:default        *proc_prologue == NULLC
	* option prologue:usermacro      *proc_prologue != NULLC
	*/
	if (ModuleInfo.prologuemode == PEM_DEFAULT)
		write_default_prologue();
	else if (ModuleInfo.prologuemode == PEM_MACRO)
		write_userdef_prologue(tokenarray);

	ProcStatus &= ~PRST_INSIDE_PROLOGUE;
	CurrProc->e.procinfo->prologueDone = TRUE;

	/* v2.10: for debug info, calculate prologue size */
	CurrProc->e.procinfo->size_prolog = GetCurrOffset() - CurrProc->sym.offset;
	return;
}

/**************************************** */
/* Pop the register when a procedure ends */
static void pop_register(uint_16 *regist)
{
	int cnt;
	if (regist == NULL)
		return;
	cnt = *regist;
	regist += cnt;
	if (ModuleInfo.win64_flags & W64F_SMART)
	{
		for (cnt = CurrProc->e.procinfo->pushed_reg; cnt; cnt--, regist--) {
			/* don't "pop" xmm registers */
			if ((GetValueSp(*regist) & OP_XMM) || (GetValueSp(*regist) & OP_YMM) || (GetValueSp(*regist) & OP_ZMM))
			{
				cnt++;
				continue;
			}
			AddLineQueueX("pop %r", *regist);
		}
	}
	else {
		for (; cnt; cnt--, regist--) {
			/* don't "pop" xmm registers */
			if ((GetValueSp(*regist) & OP_XMM) || (GetValueSp(*regist) & OP_YMM) || (GetValueSp(*regist) & OP_ZMM))
				continue;
			AddLineQueueX("pop %r", *regist);
		}
	}

}

/* write default epilogue code
* if a RET/IRET instruction has been found inside a PROC.
* epilog code timings
*
*                                                  best result
*              size  86  286  386  486  P      86  286  386  486  P
* mov sp,bp    2     2   2    2    1    1
* pop bp       2     8   5    4    4    1
*             -----------------------------
*              4     10  7    6    5    2      x             x    x
*
* mov esp,ebp  2     -   -    2    1    1
* pop ebp      2     -   -    4    4    1
*             -----------------------------
*              4     -   -    6    5    2                    x    x
*
* leave        1     -   5    4    5    3          x    x    x
*
* !!!! DECISION !!!!
*
* leave will be used for .286 and .386
* .286 code will be best working on 286,386 and 486 processors
* .386 code will be best working on 386 and 486 processors
* .486 code will be best working on 486 and above processors
*
*   without LEAVE
*
*         86  286  386  486  P
*  .8086  0   -2   -2   0    +1
*  .286   -   -2   -2   0    +1
*  .386   -   -    -2   0    +1
*  .486   -   -    -    0    +1
*
*   LEAVE 286 only
*
*         86  286  386  486  P
*  .8086  0   -2   -2   0    +1
*  .286   -   0    +2   0    -1
*  .386   -   -    -2   0    +1
*  .486   -   -    -    0    +1
*
*   LEAVE 286 and 386
*
*         86  286  386  486  P
*  .8086  0   -2   -2   0    +1
*  .286   -   0    +2   0    -1
*  .386   -   -    0    0    -1
*  .486   -   -    -    0    +1
*
*   LEAVE 286, 386 and 486
*
*         86  286  386  486  P
*  .8086  0   -2   -2   0    +1
*  .286   -   0    +2   0    -1
*  .386   -   -    0    0    -1
*  .486   -   -    -    0    -1
*/

/* Write generic epilogue for 286/386, stdcall, borland, watc etc. */
static void write_generic_epilogue(struct proc_info *info)
{
	int resstack = 0;
	int stackadj = 0;
	
	check_proc_fpo(info);

	if (ModuleInfo.Ofssize == USE64 && ModuleInfo.fctype == FCT_WIN64 && (ModuleInfo.win64_flags & W64F_AUTOSTACKSP))
	{
		resstack = sym_ReservedStack->value;
		if (Options.frameflags)
		{
			AddLineQueueX("lea %r, [%r+(%d+%s)]", stackreg[ModuleInfo.Ofssize], stackreg[ModuleInfo.Ofssize], NUMQUAL info->localsize, sym_ReservedStack->name);
		}
		else if (resstack)
		{
			AddLineQueueX("add %r, %d + %s", stackreg[ModuleInfo.Ofssize], NUMQUAL info->localsize, sym_ReservedStack->name);
		}
	}

	/* Pop the registers */
	pop_register(CurrProc->e.procinfo->regslist);

	if (info->loadds)
		AddLineQueueX("pop %r", T_DS);

	if (info->fpo)
	{
		if (info->pushed_reg % 2 == 0 && info->localsize % 16 == 0)
			stackadj = 8;
		else if (info->pushed_reg % 2 == 0 && info->localsize % 16 != 0)
			stackadj = 0;
		else if (info->pushed_reg % 2 != 0 && info->localsize % 16 == 0)
			stackadj = 0;
		else if (info->pushed_reg % 2 != 0 && info->localsize % 16 != 0)
			stackadj = 8;
	}
	else
	{
		if (info->pushed_reg % 2 == 0 && info->localsize % 16 == 0)
			stackadj = 0;
		else if (info->pushed_reg % 2 == 0 && info->localsize % 16 != 0)
			stackadj = 8;
		else if (info->pushed_reg % 2 != 0 && info->localsize % 16 == 0)
			stackadj = 8;
		else if (info->pushed_reg % 2 != 0 && info->localsize % 16 != 0)
			stackadj = 0;
	}

	if (ModuleInfo.Ofssize == USE64 && stackadj > 0 && info->fpo && !info->isleaf)
	{
		if (Options.frameflags)
		{
			AddLineQueueX("lea %r, [%r+%d]", T_RSP, stackadj);
		}
		else
		{
			AddLineQueueX("add %r, %d", T_RSP, stackadj);
		}
	}

	if ((info->locallist == NULL) && info->stackparam == FALSE && info->has_vararg == FALSE && resstack == 0 && info->forceframe == FALSE)
		return;

	/* restore registers e/sp and e/bp.
	* emit either "leave" or "mov e/sp,e/bp, pop e/bp".
	*/
	if (!(info->locallist || info->stackparam || info->has_vararg || info->forceframe))
		;
	else
	{
		if (info->pe_type && !info->fpo)
		{
			AddLineQueue("leave");
		}
		else
		{
			if (info->fpo)
			{
				if (ModuleInfo.Ofssize == USE64 && ModuleInfo.fctype == FCT_WIN64 && (ModuleInfo.win64_flags & W64F_AUTOSTACKSP))
					;
				else
				{
					if (Options.frameflags)
					{
						AddLineQueueX("lea %r, [%r+%d]", stackreg[ModuleInfo.Ofssize], stackreg[ModuleInfo.Ofssize], NUMQUAL info->localsize);
					}
					else if (info->localsize)
					{
						AddLineQueueX("add %r, %d", stackreg[ModuleInfo.Ofssize], NUMQUAL info->localsize);
					}
				}
				return;
			}
			else
			{
				/*
				MOV [E|R]SP, [E|R]BP
				POP [E|R]BP
				*/
				if (info->localsize != 0)
				{
					AddLineQueueX("mov %r, %r", stackreg[ModuleInfo.Ofssize], info->basereg);
				}
				AddLineQueueX("pop %r", info->basereg);
			}
		}

	}
}

static void write_default_epilogue(void)
/****************************************/
{
	struct proc_info   *info;
	info = CurrProc->e.procinfo;

	if (ModuleInfo.Ofssize == USE64)
	{
		if (ModuleInfo.basereg[USE64] == T_RSP && (CurrProc->sym.langtype == LANG_FASTCALL || CurrProc->sym.langtype == LANG_VECTORCALL))
			write_win64_default_epilogue_RSP(info);
		else if (ModuleInfo.basereg[USE64] == T_RBP && CurrProc->sym.langtype == LANG_FASTCALL && info->isframe)
			write_win64_default_epilogue_RBP(info); /* UASM win64:N style epilogue */
		else if (ModuleInfo.basereg[USE64] == T_RBP && CurrProc->sym.langtype == LANG_FASTCALL)
			write_generic_epilogue(info);
		else if (ModuleInfo.basereg[USE64] == T_RBP && CurrProc->sym.langtype == LANG_SYSVCALL)
			write_sysv_default_epilogue_RBP(info);
	}
	else
		write_generic_epilogue(info);
	return;
}

/* write userdefined epilogue code
* if a RET/IRET instruction has been found inside a PROC.
*/
static ret_code write_userdef_epilogue(bool flag_iret, struct asm_tok tokenarray[])
/***********************************************************************************/
{
	uint_16 *regs;
	int i;
	char *p;
	bool is_exitm;
	struct proc_info   *info;
	int flags = CurrProc->sym.langtype; /* set bits 0-2 */
	struct dsym *dir;
	char reglst[128];
	char buffer[MAX_LINE_LEN]; /* stores string for RunMacro() */

	dir = (struct dsym *)SymSearch(ModuleInfo.proc_epilogue);
	if (dir == NULL ||
		dir->sym.state != SYM_MACRO ||
		dir->sym.isfunc == TRUE) {
		return(EmitErr(EPILOGUE_MUST_BE_MACRO_PROC, ModuleInfo.proc_epilogue));
	}

	info = CurrProc->e.procinfo;

#if AMD64_SUPPORT
	/* to be compatible with ML64, translate FASTCALL to 0 (not 7) */
	if (CurrProc->sym.langtype == LANG_FASTCALL && ModuleInfo.fctype == FCT_WIN64)
		flags = 0;
#endif
	if (CurrProc->sym.langtype == LANG_C ||
		CurrProc->sym.langtype == LANG_SYSCALL ||
		CurrProc->sym.langtype == LANG_FASTCALL ||
		CurrProc->sym.langtype == LANG_SYSVCALL)
		flags |= 0x10;

	flags |= (CurrProc->sym.mem_type == MT_FAR ? 0x20 : 0);
	flags |= (CurrProc->sym.ispublic ? 0 : 0x40);
	/* v2.11: set bit 7, the export flag */
	flags |= (info->isexport ? 0x80 : 0);
	flags |= flag_iret ? 0x100 : 0;  /* bit 8: 1 if IRET    */

	p = reglst;
	if (info->regslist) {
		int cnt = *info->regslist;
		regs = info->regslist + cnt;
		for (; cnt; regs--, cnt--) {
			GetResWName(*regs, p);
			p += strlen(p);
			if (cnt != 1)
				*p++ = ',';
		}
	}
	*p = NULLC;
	//strcat( reglst, ">" );

	/* v2.07: make the numeric arguments more Masm-compatible */
	//sprintf( buffer,"%s %s, %02XH, %02XH, %02XH, <<%s>>, <%s>", ModuleInfo.proc_epilogue,
	sprintf(buffer, "%s, 0%XH, 0%XH, 0%XH, <<%s>>, <%s>",
		CurrProc->sym.name, flags, info->parasize, info->localsize,
		reglst, info->prologuearg ? info->prologuearg : "");
	i = Token_Count + 1;
	Tokenize(buffer, i, tokenarray, TOK_RESCAN);

	/* if -EP is on, emit "epilogue: none" */
	if (Options.preprocessor_stdout)
		printf("option epilogue:none\n");

	RunMacro(dir, i, tokenarray, NULL, 0, &is_exitm);

	Token_Count = i - 1;
	return(NOT_ERROR);
}

/* a RET <nnnn> or IRET/IRETD has occured inside a PROC.
* count = number of tokens in buffer (=Token_Count)
* it's ensured already that ModuleInfo.proc_epilogue isn't NULL.
*/
ret_code RetInstr(int i, struct asm_tok tokenarray[], int count)
/****************************************************************/
{
	struct proc_info   *info;
	bool        is_iret = FALSE;
	char        *p;
#ifdef DEBUG_OUT
	ret_code    rc;
#endif
	char        buffer[MAX_LINE_LEN]; /* stores modified RETN/RETF/IRET instruction */

#if AMD64_SUPPORT
	if (tokenarray[i].tokval == T_IRET || tokenarray[i].tokval == T_IRETD || tokenarray[i].tokval == T_IRETQ)
#else
	if (tokenarray[i].tokval == T_IRET || tokenarray[i].tokval == T_IRETD)
#endif
		is_iret = TRUE;

	if (ModuleInfo.epiloguemode == PEM_MACRO) {
#if FASTPASS
		/* don't run userdefined epilogue macro if pass > 1 */
		if (UseSavedState) {
			if (Parse_Pass > PASS_1) {
				DebugMsg(("RetInstr() exit\n"));
				//return( NOT_ERROR );
				return(ParseLine(tokenarray));
			}
			/* handle the current line as if it is REPLACED by the macro content */
			*(LineStoreCurr->line) = ';';
		}
#endif
#ifdef DEBUG_OUT
		rc = write_userdef_epilogue(is_iret, tokenarray);
		DebugMsg(("RetInstr() exit\n"));
		return(rc);
#else
		return(write_userdef_epilogue(is_iret, tokenarray));
#endif
	}

	if (ModuleInfo.list) {
		LstWrite(LSTTYPE_DIRECTIVE, GetCurrOffset(), NULL);
	}

	/* If the ret instruction had bnd, add prefix */
	if (tokenarray[0].tokval == T_BND)
	{
		strcpy(buffer, "bnd ");
		strcpy(buffer + 4, tokenarray[i].string_ptr);
	}
	else
		strcpy(buffer, tokenarray[i].string_ptr);
	p = buffer + strlen(buffer);

	/* Only write epilogue if not PEM_NONE */
	if (ModuleInfo.epiloguemode == PEM_DEFAULT)
		write_default_epilogue();

	info = CurrProc->e.procinfo;

	/* UASM 2.42 - Any proc with no prologue will have no stack frame, so set fpo and force use of esp/rsp if option stackbase:xSP is set */
	if (ModuleInfo.epiloguemode == PEM_NONE && CurrProc->e.procinfo->forceframe == FALSE && (CurrProc->e.procinfo->basereg == T_ESP))
	{
		if (ModuleInfo.Ofssize == USE64 && CurrProc->e.procinfo->localsize > 0)
			AddLineQueueX("add rsp,%d", CurrProc->e.procinfo->localsize);
		else if (CurrProc->e.procinfo->localsize > 0)
			AddLineQueueX("add esp,%d", CurrProc->e.procinfo->localsize);

		RunLineQueue();
		//return;
	}

	/* skip this part for IRET */
	if (is_iret == FALSE) 
	{
		if (CurrProc->e.procinfo->basereg == T_ESP || CurrProc->e.procinfo->basereg == T_RSP)
		{
			if (CurrProc->sym.mem_type == MT_FAR)
				*p++ = 'f';   /* ret -> retf */
			else if ((*(p - 1)) != 'n')
				*p++ = 'n';     /* ret -> retn */
		}
		else
		{
			if (CurrProc->sym.mem_type == MT_FAR)
				*p++ = 'f';   /* ret -> retf */
			else
				*p++ = 'n';     /* ret -> retn */
		}
	}
	i++; /* skip directive */
	if (info->parasize || (count != i))
		*p++ = ' ';
	*p = NULLC;
	/* RET without argument? Then calculate the value */
	if (is_iret == FALSE && count == i) {
		if (ModuleInfo.epiloguemode != PEM_NONE) {
			switch (CurrProc->sym.langtype) {
			case LANG_BASIC:
			case LANG_FORTRAN:
			case LANG_PASCAL:
				if (info->parasize != 0) {
					sprintf(p, "%d%c", info->parasize, ModuleInfo.radix != 10 ? 't' : NULLC);
				}
				break;
			case LANG_FASTCALL:
				fastcall_tab[ModuleInfo.fctype].handlereturn(CurrProc, buffer);
				break;
			case LANG_VECTORCALL:
				vectorcall_tab[ModuleInfo.fctype].handlereturn(CurrProc, buffer);
				break;
			case LANG_SYSVCALL:
				sysvcall_tab[ModuleInfo.fctype].handlereturn(CurrProc, buffer);
				break;
			case LANG_STDCALL:
				if (!info->has_vararg && info->parasize != 0) {
					sprintf(p, "%d%c", info->parasize, ModuleInfo.radix != 10 ? 't' : NULLC);
				}
				break;
			case LANG_DELPHICALL:
				if (info->ReservedStack > 0) {
					sprintf(p, "%d%c", info->ReservedStack, ModuleInfo.radix != 10 ? 't' : NULLC);
				}
				break;
			}
		}
	}
	else {
		/* v2.04: changed. Now works for both RET nn and IRETx */
		/* v2.06: changed. Now works even if RET has ben "renamed" */
		strcpy(p, tokenarray[i].tokpos);
	}
	AddLineQueue(buffer);
	RunLineQueue();

	return(NOT_ERROR);
}

/* init this module. called for every pass. */

void ProcInit(void)
/*******************/
{
	ProcStack = NULL;
	CurrProc = NULL;
	procidx = 1;
	ProcStatus = 0;
	/* v2.09: reset prolog and epilog mode */
	ModuleInfo.prologuemode = PEM_DEFAULT;
	ModuleInfo.epiloguemode = PEM_DEFAULT;
	/* v2.06: no forward references in INVOKE if -Zne is set */
	ModuleInfo.invoke_exprparm = (Options.strict_masm_compat ? EXPF_NOUNDEF : 0);
	ModuleInfo.basereg[USE16] = T_BP;
	ModuleInfo.basereg[USE32] = T_EBP;
	ModuleInfo.basereg[USE64] = T_RBP;
	unw_segs_defined = 0;
}