1 // SPDX-License-Identifier: GPL-2.0
25 # error This test is 64-bit only
111 	uint32_t eax, ebx, ecx, edx;  in check_cpuid_xtiledata()  local
114 		      eax, ebx, ecx, edx);  in check_cpuid_xtiledata()
126 		      eax, ebx, ecx, edx);  in check_cpuid_xtiledata()
145 	/* XSAVE buffer should be 64B-aligned. */  in alloc_xbuf()
154 	memset(&buffer->header, 0, sizeof(buffer->header));  in clear_xstate_header()
160 	*(uint64_t *)(&buffer->header) = bv;  in set_xstatebv()
165 	int *ptr = (int *)&xbuf->bytes[xtiledata.xbuf_offset];  in set_rand_tiledata()
211 #define SIGNAL_BUF_LEN 1000
215 	int left = SIGNAL_BUF_LEN - strlen(signal_message_buffer) - 1;  in sig_print()
229 	void *xbuf = ctx->uc_mcontext.fpregs;  in handle_noperm()
237 	if (si->si_code != ILL_ILLOPC) {  in handle_noperm()
254 	if (sw_bytes->xstate_size <= xtiledata.xbuf_offset) {  in handle_noperm()
274 	ctx->uc_mcontext.gregs[REG_RIP] += 3; /* Skip the faulting XRSTOR */  in handle_noperm()
398 			MAP_PRIVATE | MAP_ANONYMOUS | MAP_STACK, -1, 0);  in alloc_altstack()
456 	small_size = minsigstksz - xtiledata.size;  in test_dynamic_sigaltstack()
472 	 * too-small altstack.  This ensures that big-enough  in test_dynamic_sigaltstack()
473 	 * sigaltstacks can not shrink to a too-small value  in test_dynamic_sigaltstack()
516 	 * XTILEDATA-compatible signal stack  in test_dynamic_state()
522 	 * Set up an XTILEDATA-compatible signal stack and  in test_dynamic_state()
560 	return memcmp(&xbuf1->bytes[xtiledata.xbuf_offset],  in __compare_tiledata_state()
561 		      &xbuf2->bytes[xtiledata.xbuf_offset],  in __compare_tiledata_state()
684 		pthread_mutex_lock(&finfo->mutex);  in check_tiledata()
704 		pthread_mutex_unlock(&finfo->next->mutex);  in check_tiledata()
822  * functions. So, the tester is advised to double-check any emitted
853 	memcpy(&stashed_xsave->bytes[xtiledata.xbuf_offset],  in ptracer_inject_tiledata()
854 	       &xbuf->bytes[xtiledata.xbuf_offset],  in ptracer_inject_tiledata()