1 // SPDX-License-Identifier: GPL-2.0
25 # error This test is 64-bit only
108 	uint32_t eax, ebx, ecx, edx;  in check_cpuid_xsave()  local
111 	 * CPUID.1:ECX.XSAVE[bit 26] enumerates general  in check_cpuid_xsave()
115 	__cpuid_count(1, 0, eax, ebx, ecx, edx);  in check_cpuid_xsave()
116 	if (!(ecx & CPUID_LEAF1_ECX_XSAVE_MASK))  in check_cpuid_xsave()
118 	if (!(ecx & CPUID_LEAF1_ECX_OSXSAVE_MASK))  in check_cpuid_xsave()
136 	uint32_t eax, ebx, ecx, edx;  in check_cpuid_xtiledata()  local
139 		      eax, ebx, ecx, edx);  in check_cpuid_xtiledata()
151 		      eax, ebx, ecx, edx);  in check_cpuid_xtiledata()
170 	/* XSAVE buffer should be 64B-aligned. */  in alloc_xbuf()
179 	memset(&buffer->header, 0, sizeof(buffer->header));  in clear_xstate_header()
185 	return *(uint64_t *)&buffer->header;  in get_xstatebv()
191 	*(uint64_t *)(&buffer->header) = bv;  in set_xstatebv()
196 	int *ptr = (int *)&xbuf->bytes[xtiledata.xbuf_offset];  in set_rand_tiledata()
242 #define SIGNAL_BUF_LEN 1000
246 	int left = SIGNAL_BUF_LEN - strlen(signal_message_buffer) - 1;  in sig_print()
260 	void *xbuf = ctx->uc_mcontext.fpregs;  in handle_noperm()
268 	if (si->si_code != ILL_ILLOPC) {  in handle_noperm()
285 	if (sw_bytes->xstate_size <= xtiledata.xbuf_offset) {  in handle_noperm()
305 	ctx->uc_mcontext.gregs[REG_RIP] += 3; /* Skip the faulting XRSTOR */  in handle_noperm()
428 			MAP_PRIVATE | MAP_ANONYMOUS | MAP_STACK, -1, 0);  in alloc_altstack()
486 	small_size = minsigstksz - xtiledata.size;  in test_dynamic_sigaltstack()
502 	 * too-small altstack.  This ensures that big-enough  in test_dynamic_sigaltstack()
503 	 * sigaltstacks can not shrink to a too-small value  in test_dynamic_sigaltstack()
546 	 * XTILEDATA-compatible signal stack  in test_dynamic_state()
552 	 * Set up an XTILEDATA-compatible signal stack and  in test_dynamic_state()
590 	return memcmp(&xbuf1->bytes[xtiledata.xbuf_offset],  in __compare_tiledata_state()
591 		      &xbuf2->bytes[xtiledata.xbuf_offset],  in __compare_tiledata_state()
714 		pthread_mutex_lock(&finfo->mutex);  in check_tiledata()
734 		pthread_mutex_unlock(&finfo->next->mutex);  in check_tiledata()
852  * functions. So, the tester is advised to double-check any emitted
883 	memcpy(&stashed_xsave->bytes[xtiledata.xbuf_offset],  in ptracer_inject_tiledata()
884 	       &xbuf->bytes[xtiledata.xbuf_offset],  in ptracer_inject_tiledata()