62 #define fatal_error(msg, ...)	err(1, "[FAIL]\t" msg, ##__VA_ARGS__)  macro
74 		fatal_error("sigaction");  in sethandler()
85 		fatal_error("sigaction");  in clearhandler()
132 		fatal_error("xstate cpuid: invalid tile data size/offset: %d/%d",  in check_cpuid_xtiledata()
148 		fatal_error("aligned_alloc()");  in alloc_xbuf()
186 		fatal_error("failed to allocate stashed_xsave\n");  in init_stashed_xsave()
292 		fatal_error("saw %d errors in noperm signal handler\n", noperm_errs);  in xrstor_safe()
338 		fatal_error("prctl(ARCH_GET_XCOMP_PERM) error: %ld", rc);  in validate_req_xcomp_perm()
340 		fatal_error("ARCH_GET_XCOMP_PERM returns XFEATURE_XTILECFG off.");  in validate_req_xcomp_perm()
350 		fatal_error("ARCH_REQ_XCOMP_PERM saw unexpected success.\n");  in validate_req_xcomp_perm()
352 		fatal_error("ARCH_REQ_XCOMP_PERM saw unexpected failure.\n");  in validate_req_xcomp_perm()
359 		fatal_error("prctl(ARCH_GET_XCOMP_PERM) error: %ld", rc);  in validate_req_xcomp_perm()
361 		fatal_error("ARCH_REQ_XCOMP_PERM set a wrong bitmask: %lx, expected: %lx.\n",  in validate_req_xcomp_perm()
401 		fatal_error("mmap() for altstack");  in alloc_altstack()
421 			fatal_error("sigaltstack() succeeded unexpectedly.\n");  in setup_altstack()
424 		fatal_error("sigaltstack()");  in setup_altstack()
487 		fatal_error("fork");  in test_dynamic_state()
494 			fatal_error("arch_prctl test parent exit");  in test_dynamic_state()
504 		fatal_error("fork");  in test_dynamic_state()
510 			fatal_error("arch_prctl test child exit");  in test_dynamic_state()
536 		fatal_error("fork");  in test_dynamic_state()
552 			fatal_error("fork test grandchild");  in test_dynamic_state()
578 		fatal_error("failed to allocate XSAVE buffer\n");  in __validate_tiledata_regs()
595 		fatal_error("TILEDATA registers changed");  in validate_tiledata_regs_same()
603 		fatal_error("TILEDATA registers did not change");  in validate_tiledata_regs_changed()
615 		fatal_error("fork");  in test_fork()
622 			fatal_error("fork test child");  in test_fork()
633 		fatal_error("fork");  in test_fork()
640 			fatal_error("fork test grand child");  in test_fork()
676 		fatal_error("unable to allocate XSAVE buffer");  in check_tiledata()
735 			fatal_error("pthread_create()");  in create_threads()
748 		fatal_error("sched_setaffinity to CPU 0");  in affinitize_cpu0()
768 		fatal_error("malloc()");  in test_context_switch()
792 			fatal_error("pthread_join() failed for thread %d err: %d\n",  in test_context_switch()
796 			fatal_error("unexpected thread retval for thread %d: %p\n",  in test_context_switch()
832 		fatal_error("unable to allocate XSAVE buffer");  in ptracer_inject_tiledata()
842 		fatal_error("PTRACE_GETREGSET");  in ptracer_inject_tiledata()
858 		fatal_error("PTRACE_SETREGSET");  in ptracer_inject_tiledata()
861 		fatal_error("PTRACE_GETREGSET");  in ptracer_inject_tiledata()