Microsoft MVP성태의 닷넷 이야기
VC++: 88. 하룻밤의 꿈 - 인텔 하스웰의 TSX Instruction 지원 [링크 복사], [링크+제목 복사],
조회: 25771
글쓴 사람
정성태 (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" 예외가 발생하는 사례를 소개합니다.
정성태

... 91  92  93  94  95  96  97  98  99  100  101  102  103  104  [105]  ...
NoWriterDateCnt.TitleFile(s)
11367정성태11/25/201729910개발 환경 구성: 337. 윈도우 운영체제의 route 명령어 사용법
11366정성태11/25/201721962오류 유형: 430. 이벤트 로그 - Cryptographic Services failed while processing the OnIdentity() call in the System Writer Object.
11365정성태11/25/201722890오류 유형: 429. 이벤트 로그 - User Policy could not be updated successfully
11364정성태11/24/201726371사물인터넷: 11. Raspberry Pi Zero(OTG)를 다른 컴퓨터에 연결해 가상 마우스로 쓰는 방법 (절대 좌표) [2]
11363정성태11/23/201726289사물인터넷: 10. Raspberry Pi Zero(OTG)를 다른 컴퓨터에 연결해 가상 마우스 + 키보드로 쓰는 방법 (두 번째 이야기)
11362정성태11/22/201720982오류 유형: 428. 윈도우 업데이트 KB4048953 - 0x800705b4 [2]
11361정성태11/22/201724299오류 유형: 427. 이벤트 로그 - Filter Manager failed to attach to volume '\Device\HarddiskVolume??' 0xC03A001C
11360정성태11/22/201725248오류 유형: 426. 이벤트 로그 - The kernel power manager has initiated a shutdown transition.
11359정성태11/16/201724195오류 유형: 425. 윈도우 10 Version 1709 (OS Build 16299.64) 업그레이드 시 발생한 문제 2가지
11358정성태11/15/201729489사물인터넷: 9. Visual Studio 2017에서 Raspberry Pi C++ 응용 프로그램 제작 [1]
11357정성태11/15/201729905개발 환경 구성: 336. 윈도우 10 Bash 쉘에서 C++ 컴파일하는 방법
11356정성태11/15/201731485사물인터넷: 8. Raspberry Pi Zero(OTG)를 다른 컴퓨터에 연결해 가상 마우스 + 키보드로 쓰는 방법 [4]
11355정성태11/15/201726071사물인터넷: 7. Raspberry Pi Zero(OTG)를 다른 컴퓨터에 연결해 가상 마우스로 쓰는 방법 [2]파일 다운로드2
11354정성태11/14/201731412사물인터넷: 6. Raspberry Pi Zero(OTG)를 다른 컴퓨터에 연결해 가상 키보드로 쓰는 방법 [8]
11353정성태11/14/201728268사물인터넷: 5. Raspberry Pi Zero(OTG)를 다른 컴퓨터에 연결해 가상 이더넷 카드로 쓰는 방법 [1]
11352정성태11/14/201725016사물인터넷: 4. Samba를 이용해 윈도우와 Raspberry Pi간의 파일 교환 [1]
11351정성태11/7/201727362.NET Framework: 698. C# 컴파일러 대신 직접 구현하는 비동기(async/await) 코드 [6]파일 다운로드1
11350정성태11/1/201723413디버깅 기술: 108. windbg 분석 사례 - Redis 서버로의 호출을 기다리면서 hang 현상 발생
11349정성태10/31/201724643디버깅 기술: 107. windbg - x64 SOS 확장의 !clrstack 명령어가 출력하는 Child SP 값의 의미 [1]파일 다운로드1
11348정성태10/31/201720338디버깅 기술: 106. windbg - x64 역어셈블 코드에서 닷넷 메서드 호출의 인자를 확인하는 방법
11347정성태10/28/201724286오류 유형: 424. Visual Studio - "클래스 다이어그램 보기" 시 "작업을 완료할 수 없습니다. 해당 인터페이스를 지원하지 않습니다." 오류 발생
11346정성태10/25/201721071오류 유형: 423. Windows Server 2003 - The client-side extension could not remove user policy settings for 'Default Domain Policy {...}' (0x8007000d)
11338정성태10/25/201717792.NET Framework: 697. windbg - SOS DumpMT의 "BaseSize", "ComponentSize" 값에 대한 의미파일 다운로드1
11337정성태10/24/201720797.NET Framework: 696. windbg - SOS DumpClass/DumpMT의 "Vtable Slots", "Total Method Slots", "Slots in VTable" 값에 대한 의미파일 다운로드1
11336정성태10/20/201722454.NET Framework: 695. windbg - .NET string의 x86/x64 메모리 할당 구조
11335정성태10/18/201721085.NET Framework: 694. 닷넷 - <Module> 클래스의 용도
... 91  92  93  94  95  96  97  98  99  100  101  102  103  104  [105]  ...