1 // SPDX-License-Identifier: GPL-2.0
23 # error This test is 64-bit only
142 	 * components corresponding to bits currently set in XCR0.  in check_cpuid_xtiledata()
168 	/* XSAVE buffer should be 64B-aligned. */  in alloc_xbuf()
177 	memset(&buffer->header, 0, sizeof(buffer->header));  in clear_xstate_header()
183 	return *(uint64_t *)&buffer->header;  in get_xstatebv()
189 	*(uint64_t *)(&buffer->header) = bv;  in set_xstatebv()
194 	int *ptr = (int *)&xbuf->bytes[xtiledata.xbuf_offset];  in set_rand_tiledata()
244 	int left = SIGNAL_BUF_LEN - strlen(signal_message_buffer) - 1;  in sig_print()
258 	void *xbuf = ctx->uc_mcontext.fpregs;  in handle_noperm()
266 	if (si->si_code != ILL_ILLOPC) {  in handle_noperm()
283 	if (sw_bytes->xstate_size <= xtiledata.xbuf_offset) {  in handle_noperm()
303 	ctx->uc_mcontext.gregs[REG_RIP] += 3; /* Skip the faulting XRSTOR */  in handle_noperm()
426 			MAP_PRIVATE | MAP_ANONYMOUS | MAP_STACK, -1, 0);  in alloc_altstack()
436 	stack_t ss;  in setup_altstack()  local
439 	memset(&ss, 0, sizeof(ss));  in setup_altstack()
440 	ss.ss_size = size;  in setup_altstack()
441 	ss.ss_sp = addr;  in setup_altstack()
443 	rc = sigaltstack(&ss, NULL);  in setup_altstack()
484 	small_size = minsigstksz - xtiledata.size;  in test_dynamic_sigaltstack()
500 	 * too-small altstack.  This ensures that big-enough  in test_dynamic_sigaltstack()
501 	 * sigaltstacks can not shrink to a too-small value  in test_dynamic_sigaltstack()
544 	 * XTILEDATA-compatible signal stack  in test_dynamic_state()
550 	 * Set up an XTILEDATA-compatible signal stack and  in test_dynamic_state()
602 	ret = memcmp(&xbuf1->bytes[xtiledata.xbuf_offset],  in __validate_tiledata_regs()
603 		     &xbuf2->bytes[xtiledata.xbuf_offset],  in __validate_tiledata_regs()
707 		pthread_mutex_lock(&finfo->mutex);  in check_tiledata()
727 		pthread_mutex_unlock(&finfo->next->mutex);  in check_tiledata()
738 static int create_threads(int num, struct futex_info *finfo)  in create_threads()  argument
742 	for (i = 0; i < num; i++) {  in create_threads()
754 		next_nr = (i + 1) % num;  in create_threads()