Microsoft MVP성태의 닷넷 이야기
VC++: 88. 하룻밤의 꿈 - 인텔 하스웰의 TSX Instruction 지원 [링크 복사], [링크+제목 복사],
조회: 25704
글쓴 사람
정성태 (techsharer at outlook.com)
홈페이지
첨부 파일
 

하룻밤의 꿈 - 인텔 하스웰의 TSX Instruction 지원

예전에 아래의 글에서 잠시 TSX 관련 이야기를 했었지요. ^^

lock-free 방식이 과연 성능에 얼마나 도움이 될까요?
; https://www.sysnet.pe.kr/2/0/1458

당연히 하스웰(Haswell)부터 되고 있겠거니 생각하는 중에... 아래의 글을 보게 되었습니다. ^^

TSX Instruction 지원 cpu는 과연 
; http://www.gamecodi.com/board/zboard.php?id=GAMECODI_Talkdev&page=1&sn1=&divpage=1&sn=off&ss=on&sc=on&select_arrange=headnum&desc=asc&no=3115

위의 덧글에 보면 엔하위키 출처의,

인텔 하스웰 마이크로아키텍처
; https://mirror.enha.kr/wiki/%EC%9D%B8%ED%85%94%20%ED%95%98%EC%8A%A4%EC%9B%B0%20%EB%A7%88%EC%9D%B4%ED%81%AC%EB%A1%9C%EC%95%84%ED%82%A4%ED%85%8D%EC%B2%98

실리콘 레벨의 버그로 인해 인텔에서 TSX disable patch 배포로 사용할수없다.

라는 내용이 있습니다. 실제로 현재 다음의 코드를,

#include "stdafx.h"
#include <immintrin.h>

int _tmain(int argc, _TCHAR* argv[])
{
    unsigned int result = _xbegin();
    if (result == _XBEGIN_STARTED)
    {
        // do transaction code 
        // ...

        _xend();
    }
    else if (result == _XABORT_DEBUG) // _XABORT_DEBUG == Transaction abort due to a debug trap 
    {
        printf("_XABORT_DEBUG\n");
    }

    return 0;
}

하스웰 아키텍쳐 지원의 CPU에서 실행하면 그냥 _XABORT_DEBUG(0x16) 값만을 반환합니다.

물론, 당연하겠지만 하스웰 지원이 안되는 컴퓨터에서 실행하는 경우에는 다음과 같이 "Illegal Instruction" 예외가 발생합니다.

The exception Illegal Instruction
An attempt was made to execute an illegal instruction.
(0xc000001d) occurred in the application at location 0x010013aa.

안타깝군요... 벤치마크 자료를 보면 꽤나 훌륭했던 것으로 보이는데...

Benchmarks : Haswell's TSX and Memory Transaction Throughput (HLE and RTM)
; http://www.sisoftware.co.uk/?d=qa&f=ben_mem_hle

어쨌든, 버그가 있으면 아무리 성능이 좋아도 소용이 없는 노릇입니다. ^^




[이 글에 대해서 여러분들과 의견을 공유하고 싶습니다. 틀리거나 미흡한 부분 또는 의문 사항이 있으시면 언제든 댓글 남겨주십시오.]







[최초 등록일: ]
[최종 수정일: 2/5/2015]

Creative Commons License
이 저작물은 크리에이티브 커먼즈 코리아 저작자표시-비영리-변경금지 2.0 대한민국 라이센스에 따라 이용하실 수 있습니다.
by SeongTae Jeong, mailto:techsharer at outlook.com

비밀번호

댓글 작성자
 



2015-02-07 07시20분
[Lyn] 아쉽게도 브로드웰에서도 고쳐지지 않았습니다.

스카이레이크 기다려야할듯
[guest]
2015-02-09 03시01분
과연, 어렵긴한가 보군요. ^^ 어쨌든, 하드웨어의 클럭 경쟁이 어려워지니 이런 유의 구현으로 확장하는 것도 재미있는 현상인 것 같습니다.
정성태
2025-07-20 02시21분
The case of the invalid instruction exception on an instruction that should never have executed
; https://devblogs.microsoft.com/oldnewthing/20250718-00/?p=111390

C++의 inline 최적화로 인해 "Illegal Instruction" 예외가 발생하는 사례를 소개합니다.
정성태

... 46  47  48  49  50  51  52  53  54  55  56  57  [58]  59  60  ...
NoWriterDateCnt.TitleFile(s)
12550정성태3/5/202116643오류 유형: 701. Live Share 1.0.3713.0 버전을 1.0.3884.0으로 업데이트 이후 ContactServiceModelPackage 오류 발생하는 문제
12549정성태3/4/202118419오류 유형: 700. VsixPublisher를 이용한 등록 시 다양한 오류 유형 해결책
12548정성태3/4/202119525개발 환경 구성: 546. github workflow/actions에서 nuget 패키지 등록하는 방법
12547정성태3/3/202120041오류 유형: 699. 비주얼 스튜디오 - The 'CascadePackage' package did not load correctly.
12546정성태3/3/202120251개발 환경 구성: 545. github workflow/actions에서 빌드시 snk 파일 다루는 방법 - Encrypted secrets
12545정성태3/2/202122731.NET Framework: 1026. 닷넷 5에 추가된 POH (Pinned Object Heap) [10]
12544정성태2/26/202123163.NET Framework: 1025. C# - Control의 Invalidate, Update, Refresh 차이점 [2]
12543정성태2/26/202120665VS.NET IDE: 158. C# - 디자인 타임(design-time)과 런타임(runtime)의 코드 실행 구분
12542정성태2/20/202122198개발 환경 구성: 544. github repo의 Release 활성화 및 Actions를 이용한 자동화 방법 [1]
12541정성태2/18/202119787개발 환경 구성: 543. 애저듣보잡 - Github Workflow/Actions 소개
12540정성태2/17/202121405.NET Framework: 1024. C# - Win32 API에 대한 P/Invoke를 대신하는 Microsoft.Windows.CsWin32 패키지
12539정성태2/16/202121326Windows: 189. WM_TIMER의 동작 방식 개요파일 다운로드1
12538정성태2/15/202121941.NET Framework: 1023. C# - GC 힙이 아닌 Native 힙에 인스턴스 생성 - 0SuperComicLib.LowLevel 라이브러리 소개 [2]
12537정성태2/11/202121083.NET Framework: 1022. UI 요소의 접근은 반드시 그 UI를 만든 스레드에서! - 두 번째 이야기 [2]
12536정성태2/9/202120370개발 환경 구성: 542. BDP(Bandwidth-delay product)와 TCP Receive Window
12535정성태2/9/202119520개발 환경 구성: 541. Wireshark로 확인하는 LSO(Large Send Offload), RSC(Receive Segment Coalescing) 옵션
12534정성태2/8/202120402개발 환경 구성: 540. Wireshark + C/C++로 확인하는 TCP 연결에서의 closesocket 동작 [1]파일 다운로드1
12533정성태2/8/202118520개발 환경 구성: 539. Wireshark + C/C++로 확인하는 TCP 연결에서의 shutdown 동작파일 다운로드1
12532정성태2/6/202120655개발 환경 구성: 538. Wireshark + C#으로 확인하는 ReceiveBufferSize(SO_RCVBUF), SendBufferSize(SO_SNDBUF) [3]
12531정성태2/5/202119056개발 환경 구성: 537. Wireshark + C#으로 확인하는 PSH flag와 Nagle 알고리듬파일 다운로드1
12530정성태2/4/202122090개발 환경 구성: 536. Wireshark + C#으로 확인하는 TCP 통신의 Receive Window
12529정성태2/4/202121106개발 환경 구성: 535. Wireshark + C#으로 확인하는 TCP 통신의 MIN RTO [1]
12528정성태2/1/202121474개발 환경 구성: 534. Wireshark + C#으로 확인하는 TCP 통신의 MSS(Maximum Segment Size) - 윈도우 환경
12527정성태2/1/202121370개발 환경 구성: 533. Wireshark + C#으로 확인하는 TCP 통신의 MSS(Maximum Segment Size) - 리눅스 환경파일 다운로드1
12526정성태2/1/202117893개발 환경 구성: 532. Azure Devops의 파이프라인 빌드 시 snk 파일 다루는 방법 - Secure file
12525정성태2/1/202116448개발 환경 구성: 531. Azure Devops - 파이프라인 실행 시 빌드 이벤트를 생략하는 방법
... 46  47  48  49  50  51  52  53  54  55  56  57  [58]  59  60  ...