Microsoft MVP성태의 닷넷 이야기
VC++: 88. 하룻밤의 꿈 - 인텔 하스웰의 TSX Instruction 지원 [링크 복사], [링크+제목 복사],
조회: 23279
글쓴 사람
정성태 (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분
과연, 어렵긴한가 보군요. ^^ 어쨌든, 하드웨어의 클럭 경쟁이 어려워지니 이런 유의 구현으로 확장하는 것도 재미있는 현상인 것 같습니다.
정성태

... 61  62  63  64  65  66  67  [68]  69  70  71  72  73  74  75  ...
NoWriterDateCnt.TitleFile(s)
12233정성태6/19/202017334오류 유형: 619. SQL 서버 - The transaction log for database '...' is full due to 'LOG_BACKUP'. - 두 번째 이야기
12232정성태6/19/202016022오류 유형: 618. SharePoint - StoreBusyRetryLater 오류
12231정성태6/15/202019295.NET Framework: 911. Console/Service Application을 위한 SynchronizationContext - AsyncContext
12230정성태6/15/202018170오류 유형: 617. IMetaDataImport::GetMethodProps가 반환하는 IL 코드 주소(RVA) 문제
12229정성태6/13/202020029.NET Framework: 910. USB/IP PROJECT를 이용해 C#으로 USB Keyboard + Mouse 가상 장치 만들기 [1]
12228정성태6/12/202019453.NET Framework: 909. C# - Source Generator를 적용한 XmlCodeGenerator파일 다운로드1
12227정성태6/12/202023394오류 유형: 616. Visual Studio의 느린 업데이트 속도에 대한 원인 분석 [5]
12226정성태6/11/202021395개발 환경 구성: 493. OpenVPN의 네트워크 구성 [4]파일 다운로드1
12225정성태6/11/202019392개발 환경 구성: 492. 윈도우에 OpenVPN 설치 - 클라이언트 측 구성
12224정성태6/11/202028076개발 환경 구성: 491. 윈도우에 OpenVPN 설치 - 서버 측 구성 [1]
12223정성태6/9/202023779.NET Framework: 908. C# - Source Generator 소개 [10]파일 다운로드2
12222정성태6/3/202017308VS.NET IDE: 146. error information: "CryptQueryObject" (-2147024893/0x80070003)
12221정성태6/3/202017050Windows: 170. 비어 있지 않은 디렉터리로 symbolic link(junction) 연결하는 방법
12220정성태6/3/202020805.NET Framework: 907. C# DLL로부터 TLB 및 C/C++ 헤더 파일(TLH)을 생성하는 방법
12219정성태6/1/202019572.NET Framework: 906. C# - lock (this), lock (typeof(...))를 사용하면 안 되는 이유파일 다운로드1
12218정성태5/27/202019024.NET Framework: 905. C# - DirectX 게임 클라이언트 실행 중 키보드 입력을 감지하는 방법 [3]
12217정성태5/24/202017070오류 유형: 615. Transaction count after EXECUTE indicates a mismatching number of BEGIN and COMMIT statements. Previous count = 0, current count = 1.
12216정성태5/15/202020651.NET Framework: 904. USB/IP PROJECT를 이용해 C#으로 USB Keyboard 가상 장치 만들기 [14]파일 다운로드1
12215정성태5/12/202026595개발 환경 구성: 490. C# - (Wireshark의) USBPcap을 이용한 USB 패킷 모니터링 [10]파일 다운로드1
12214정성태5/5/202018256개발 환경 구성: 489. 정식 인증서가 있는 경우 Device Driver 서명하는 방법 (2) - UEFI/SecureBoot [1]
12213정성태5/3/202019400개발 환경 구성: 488. (User-mode 코드로 가상 USB 장치를 만들 수 있는) USB/IP PROJECT 소개
12212정성태5/1/202016605개발 환경 구성: 487. UEFI / Secure Boot 상태인지 확인하는 방법
12211정성태4/27/202019223개발 환경 구성: 486. WSL에서 Makefile로 공개된 리눅스 환경의 C/C++ 소스 코드 빌드
12210정성태4/20/202020661.NET Framework: 903. .NET Framework의 Strong-named 어셈블리 바인딩 (1) - app.config을 이용한 바인딩 리디렉션 [1]파일 다운로드1
12209정성태4/13/202017393오류 유형: 614. 리눅스 환경에서 C/C++ 프로그램이 Segmentation fault 에러가 발생한 경우 (2)
12208정성태4/12/202015955Linux: 29. 리눅스 환경에서 C/C++ 프로그램이 Segmentation fault 에러가 발생한 경우
... 61  62  63  64  65  66  67  [68]  69  70  71  72  73  74  75  ...