1 // SPDX-License-Identifier: GPL-2.0
25 # error This test is 64-bit only
119 	 * components corresponding to bits currently set in XCR0.  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()
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()
408 	stack_t ss;  in setup_altstack()  local
411 	memset(&ss, 0, sizeof(ss));  in setup_altstack()
412 	ss.ss_size = size;  in setup_altstack()
413 	ss.ss_sp = addr;  in setup_altstack()
415 	rc = sigaltstack(&ss, NULL);  in setup_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()
715 static int create_threads(int num, struct futex_info *finfo)  in create_threads()  argument
719 	for (i = 0; i < num; i++) {  in create_threads()
731 		next_nr = (i + 1) % num;  in create_threads()
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()