Lines Matching refs:xbuf
50 static inline void xsave(struct xsave_buffer *xbuf, uint64_t rfbm) in xsave() argument
56 : : "D" (xbuf), "a" (rfbm_lo), "d" (rfbm_hi) in xsave()
60 static inline void xrstor(struct xsave_buffer *xbuf, uint64_t rfbm) in xrstor() argument
66 : : "D" (xbuf), "a" (rfbm_lo), "d" (rfbm_hi)); in xrstor()
166 struct xsave_buffer *xbuf; in alloc_xbuf() local
169 xbuf = aligned_alloc(64, xbuf_size); in alloc_xbuf()
170 if (!xbuf) in alloc_xbuf()
172 return xbuf; in alloc_xbuf()
192 static void set_rand_tiledata(struct xsave_buffer *xbuf) in set_rand_tiledata() argument
194 int *ptr = (int *)&xbuf->bytes[xtiledata.xbuf_offset]; in set_rand_tiledata()
258 void *xbuf = ctx->uc_mcontext.fpregs; in handle_noperm() local
273 sw_bytes = get_fpx_sw_bytes(xbuf); in handle_noperm()
290 features = get_fpx_sw_bytes_features(xbuf); in handle_noperm()
307 static inline bool xrstor_safe(struct xsave_buffer *xbuf, uint64_t mask) in xrstor_safe() argument
310 xrstor(xbuf, mask); in xrstor_safe()
332 static inline bool load_rand_tiledata(struct xsave_buffer *xbuf) in load_rand_tiledata() argument
334 clear_xstate_header(xbuf); in load_rand_tiledata()
335 set_xstatebv(xbuf, XFEATURE_MASK_XTILEDATA); in load_rand_tiledata()
336 set_rand_tiledata(xbuf); in load_rand_tiledata()
337 return xrstor_safe(xbuf, XFEATURE_MASK_XTILEDATA); in load_rand_tiledata()
613 static inline void validate_tiledata_regs_same(struct xsave_buffer *xbuf) in validate_tiledata_regs_same() argument
615 int ret = __validate_tiledata_regs(xbuf); in validate_tiledata_regs_same()
621 static inline void validate_tiledata_regs_changed(struct xsave_buffer *xbuf) in validate_tiledata_regs_changed() argument
623 int ret = __validate_tiledata_regs(xbuf); in validate_tiledata_regs_changed()
694 struct xsave_buffer *xbuf; in check_tiledata() local
697 xbuf = alloc_xbuf(); in check_tiledata()
698 if (!xbuf) in check_tiledata()
705 load_rand_tiledata(xbuf); in check_tiledata()
713 validate_tiledata_regs_same(xbuf); in check_tiledata()
716 load_rand_tiledata(xbuf); in check_tiledata()
730 free(xbuf); in check_tiledata()