1 // SPDX-License-Identifier: GPL-2.0
25 # error This test is 64-bit only
144 	 * components corresponding to bits currently set in XCR0.  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()
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()
438 	stack_t ss;  in setup_altstack()  local
441 	memset(&ss, 0, sizeof(ss));  in setup_altstack()
442 	ss.ss_size = size;  in setup_altstack()
443 	ss.ss_sp = addr;  in setup_altstack()
445 	rc = sigaltstack(&ss, NULL);  in setup_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()
745 static int create_threads(int num, struct futex_info *finfo)  in create_threads()  argument
749 	for (i = 0; i < num; i++) {  in create_threads()
761 		next_nr = (i + 1) % num;  in create_threads()
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()